[SYCL] Enable sampler support in set_arg(s) method.

Signed-off-by: Alexey Voronov <alexey.voronov@intel.com>

Author: alexeyvoronov-intel

sycl/include/CL/sycl/handler.hpp

@@ -464,8 +464,11 @@ class handler {
                        sizeof(T), ArgIndex);
   }
 
-  //  TODO: implement when sampler class is ready
-  //  void setArgHelper(int argIndex, sampler &&arg) {}
+  void setArgHelper(int ArgIndex, sampler &&Arg) {
+    void *StoredArg = (void *)storePlainArg(Arg);
+    MArgs.emplace_back(detail::kernel_param_kind_t::kind_sampler, StoredArg,
+                       sizeof(sampler), ArgIndex);
+  }
 
   void verifySyclKernelInvoc(const kernel &SyclKernel) {
     if (is_host()) {

sycl/test/kernel-and-program/kernel-and-program.cpp

@@ -52,18 +52,16 @@ int main() {
     assert(data == 1);
 
     // OpenCL interoperability kernel invocation
-    // TODO add set_args(cl::sycl::sampler) use case once it's supported
     if (!q.is_host()) {
-      cl_int err;
-      if (0) {
+      {
+        cl_int err;
         cl::sycl::context ctx = q.get_context();
         cl_context clCtx = ctx.get();
         cl_command_queue clQ = q.get();
         cl_mem clBuffer =
             clCreateBuffer(clCtx, CL_MEM_WRITE_ONLY, sizeof(int), NULL, NULL);
         err = clEnqueueWriteBuffer(clQ, clBuffer, CL_TRUE, 0, sizeof(int),
                                    &data, 0, NULL, NULL);
-        // Kernel interoperability constructor
         assert(err == CL_SUCCESS);
         cl::sycl::program prog(ctx);
         prog.build_with_source(
@@ -101,6 +99,28 @@ int main() {
         assert(a == b + c);
       }
     }
+    {
+      cl::sycl::queue Queue;
+      if (!Queue.is_host()) {
+        cl::sycl::sampler first(
+            cl::sycl::coordinate_normalization_mode::normalized,
+            cl::sycl::addressing_mode::clamp, cl::sycl::filtering_mode::linear);
+        cl::sycl::sampler second(
+            cl::sycl::coordinate_normalization_mode::unnormalized,
+            cl::sycl::addressing_mode::clamp_to_edge,
+            cl::sycl::filtering_mode::nearest);
+        cl::sycl::program prog(Queue.get_context());
+        prog.build_with_source(
+            "kernel void sampler_args(int a, sampler_t first, "
+            "int b, sampler_t second, int c) {}\n");
+        cl::sycl::kernel krn = prog.get_kernel("sampler_args");
+
+        Queue.submit([&](cl::sycl::handler &cgh) {
+          cgh.set_args(0, first, 2, second, 3);
+          cgh.single_task(krn);
+        });
+      }
+    }
   }
   // Parallel for with range
   {