Fix tests and deprecate public method

Author: AlexeySachkov

sycl/include/sycl/handler.hpp

@@ -1909,6 +1909,7 @@ class __SYCL_EXPORT handler {
   /// (except for the host device).
   /// \param KernelFunc is a lambda that is used if device, queue is bound to,
   /// is a host device.
+  __SYCL_DEPRECATED("This overload isn't part of SYCL2020 and will be removed.")
   template <typename KernelName = detail::auto_name, typename KernelType>
   void single_task(kernel Kernel, const KernelType &KernelFunc) {
     // Ignore any set kernel bundles and use the one associated with the kernel

sycl/test-e2e/Basic/kernel_info.cpp

@@ -18,6 +18,8 @@
 using namespace sycl;
 namespace syclex = sycl::ext::oneapi;
 
+class SingleTask;
+
 auto checkExceptionIsThrown = [](auto &getInfoFunc,
                                  const std::string &refErrMsg,
                                  std::error_code refErrc) {
@@ -40,13 +42,13 @@ int main() {
   queue q;
   auto ctx = q.get_context();
   buffer<int, 1> buf(range<1>(1));
-  auto kernelID = sycl::get_kernel_id<class SingleTask>();
+  auto kernelID = sycl::get_kernel_id<SingleTask>();
   auto kb = get_kernel_bundle<bundle_state::executable>(ctx, {kernelID});
   kernel krn = kb.get_kernel(kernelID);
 
   q.submit([&](handler &cgh) {
     auto acc = buf.get_access<access::mode::read_write>(cgh);
-    cgh.single_task<class SingleTask>(krn, [=]() { acc[0] = acc[0] + 1; });
+    cgh.single_task<SingleTask>([=]() { acc[0] = acc[0] + 1; });
   });
 
   const std::string krnName = krn.get_info<info::kernel::function_name>();

sycl/test-e2e/Basic/kernel_info_attr.cpp

@@ -25,17 +25,19 @@
 using namespace sycl;
 namespace syclex = sycl::ext::oneapi;
 
+class SingleTask;
+
 int main() {
   queue q;
   auto ctx = q.get_context();
   buffer<int, 1> buf(range<1>(1));
-  auto KernelID = sycl::get_kernel_id<class SingleTask>();
+  auto KernelID = sycl::get_kernel_id<SingleTask>();
   auto KB = get_kernel_bundle<bundle_state::executable>(ctx, {KernelID});
   kernel krn = KB.get_kernel(KernelID);
 
   q.submit([&](handler &cgh) {
     auto acc = buf.get_access<access::mode::read_write>(cgh);
-    cgh.single_task<class SingleTask>(krn, [=]() { acc[0] = acc[0] + 1; });
+    cgh.single_task<SingleTask>([=]() { acc[0] = acc[0] + 1; });
   });
 
   const std::string krnAttr = krn.get_info<info::kernel::attributes>();

sycl/test-e2e/DeviceCodeSplit/split-per-kernel.cpp

@@ -26,7 +26,7 @@ int main() {
 
     Q.submit([&](sycl::handler &Cgh) {
       auto Acc = Buf.get_access<sycl::access::mode::read_write>(Cgh);
-      Cgh.single_task<Kern1>(Krn, [=]() { Acc[0] = 1; });
+      Cgh.single_task<Kern1>([=]() { Acc[0] = 1; });
     });
   }
   assert(Data == 1);
@@ -45,7 +45,7 @@ int main() {
 
     Q.submit([&](sycl::handler &Cgh) {
       auto Acc = Buf.get_access<sycl::access::mode::read_write>(Cgh);
-      Cgh.single_task<Kern2>(Krn, [=]() { Acc[0] = 2; });
+      Cgh.single_task<Kern2>([=]() { Acc[0] = 2; });
     });
   }
   assert(Data == 2);
@@ -64,7 +64,7 @@ int main() {
 
     Q.submit([&](sycl::handler &Cgh) {
       auto Acc = Buf.get_access<sycl::access::mode::read_write>(Cgh);
-      Cgh.single_task<Kern3>(Krn, [=]() { Acc[0] = 3; });
+      Cgh.single_task<Kern3>([=]() { Acc[0] = 3; });
     });
   }
   assert(Data == 3);

sycl/test-e2e/DeviceCodeSplit/split-per-source-main.cpp

@@ -31,7 +31,7 @@ int main() {
     sycl::buffer<int, 1> Buf(&Data, sycl::range<1>(1));
     Q.submit([&](sycl::handler &Cgh) {
       auto Acc = Buf.get_access<sycl::access::mode::read_write>(Cgh);
-      Cgh.single_task<File1Kern1>(Krn1, [=]() { Acc[0] = 1; });
+      Cgh.single_task<File1Kern1>([=]() { Acc[0] = 1; });
     });
   }
   assert(Data == 1);
@@ -40,7 +40,7 @@ int main() {
     sycl::buffer<int, 1> Buf(&Data, sycl::range<1>(1));
     Q.submit([&](sycl::handler &Cgh) {
       auto Acc = Buf.get_access<sycl::access::mode::read_write>(Cgh);
-      Cgh.single_task<File1Kern2>(Krn2, [=]() { Acc[0] = 2; });
+      Cgh.single_task<File1Kern2>([=]() { Acc[0] = 2; });
     });
   }
   assert(Data == 2);

sycl/test-e2e/DeviceImageBackendContent/CUDA_interop_test.cpp

@@ -7,18 +7,20 @@
 #include <sycl/detail/core.hpp>
 #include <vector>
 
+class mykernel;
+
 int main() {
   sycl::queue q;
   sycl::context ctxt = q.get_context();
-  sycl::kernel_id k_id = sycl::get_kernel_id<class mykernel>();
+  sycl::kernel_id k_id = sycl::get_kernel_id<mykernel>();
   auto bundle =
       sycl::get_kernel_bundle<sycl::bundle_state::executable>(ctxt, {k_id});
   assert(!bundle.empty());
   sycl::kernel krn = bundle.get_kernel(k_id);
   sycl::buffer<int> buf(sycl::range<1>(1));
   q.submit([&](sycl::handler &cgh) {
     sycl::accessor acc(buf, cgh);
-    cgh.single_task<class mykernel>(krn, [=]() { acc[0] = 42; });
+    cgh.single_task<mykernel>([=]() { acc[0] = 42; });
   });
   const auto img = *(bundle.begin());
   const auto bytes = img.ext_oneapi_get_backend_content();

sycl/test-e2e/DeviceImageBackendContent/basic_test.cpp

@@ -5,18 +5,20 @@
 #include <sycl/kernel_bundle.hpp>
 #include <type_traits>
 
+class mykernel;
+
 int main() {
   sycl::queue q;
   sycl::context ctxt = q.get_context();
   sycl::buffer<int> buf(sycl::range<1>(1));
-  sycl::kernel_id k_id = sycl::get_kernel_id<class mykernel>();
+  sycl::kernel_id k_id = sycl::get_kernel_id<mykernel>();
   auto bundle =
       sycl::get_kernel_bundle<sycl::bundle_state::executable>(ctxt, {k_id});
   assert(!bundle.empty());
   sycl::kernel krn = bundle.get_kernel(k_id);
   q.submit([&](sycl::handler &cgh) {
     sycl::accessor acc(buf, cgh);
-    cgh.single_task<class mykernel>(krn, [=]() { acc[0] = 42; });
+    cgh.single_task<mykernel>([=]() { acc[0] = 42; });
   });
   sycl::backend backend;
   std::vector<std::byte> bytes;

sycl/test-e2e/NewOffloadDriver/split-per-source-main.cpp

@@ -31,7 +31,7 @@ int main() {
     sycl::buffer<int, 1> Buf(&Data, sycl::range<1>(1));
     Q.submit([&](sycl::handler &Cgh) {
       auto Acc = Buf.get_access<sycl::access::mode::read_write>(Cgh);
-      Cgh.single_task<File1Kern1>(Krn1, [=]() { Acc[0] = 1; });
+      Cgh.single_task<File1Kern1>([=]() { Acc[0] = 1; });
     });
   }
   assert(Data == 1);
@@ -40,7 +40,7 @@ int main() {
     sycl::buffer<int, 1> Buf(&Data, sycl::range<1>(1));
     Q.submit([&](sycl::handler &Cgh) {
       auto Acc = Buf.get_access<sycl::access::mode::read_write>(Cgh);
-      Cgh.single_task<File1Kern2>(Krn2, [=]() { Acc[0] = 2; });
+      Cgh.single_task<File1Kern2>([=]() { Acc[0] = 2; });
     });
   }
   assert(Data == 2);