[SYCL] Remove handler::codeplay_host_task (#4426)

handler::codeplay_host_task is deprecated in SYCL 2020.
This patch depends on :
Changes in Lit Tests : intel/llvm-test-suite#428 and intel/llvm-test-suite#451
Signed-off-by: mdimakov [email protected]

Author: maximdimakov

sycl/include/CL/sycl/handler.hpp

@@ -1268,18 +1268,6 @@ class __SYCL_EXPORT handler {
     setType(detail::CG::RunOnHostIntel);
   }
 
-  template <typename FuncT>
-  __SYCL2020_DEPRECATED(
-      "codeplay_host_task() is deprecated, use host_task() instead")
-  detail::enable_if_t<
-      detail::check_fn_signature<detail::remove_reference_t<FuncT>,
-                                 void()>::value ||
-      detail::check_fn_signature<
-          detail::remove_reference_t<FuncT>,
-          void(interop_handle)>::value> codeplay_host_task(FuncT Func) {
-    host_task_impl(Func);
-  }
-
   /// Enqueues a command to the SYCL runtime to invoke \p Func once.
   template <typename FuncT>
   detail::enable_if_t<

sycl/include/CL/sycl/queue.hpp

@@ -1182,7 +1182,7 @@ event submitAssertCapture(queue &Self, event &Event, queue *SecondaryQueue,
 
     auto Acc = Buffer.get_access<mode::read, target::host_buffer>(CGH);
 
-    CGH.codeplay_host_task([=] {
+    CGH.host_task([=] {
       const detail::AssertHappened *AH = &Acc[0];
 
       // Don't use assert here as msvc will insert reference to __imp__wassert

sycl/source/detail/scheduler/scheduler_helpers.cpp

@@ -43,7 +43,7 @@ void initStream(StreamImplPtr Stream, QueueImplPtr Queue) {
         StrBufs->FlushBuf.get_access<access::mode::discard_write,
                                      access::target::host_buffer>(
             cgh, range<1>(FlushBufSize), id<1>(0));
-    cgh.codeplay_host_task([=] {
+    cgh.host_task([=] {
       char *FlushBufPtr = FlushBufAcc.get_pointer();
       std::memset(FlushBufPtr, 0, FlushBufAcc.get_size());
     });

sycl/source/detail/stream_impl.cpp

@@ -85,7 +85,7 @@ void stream_impl::flush() {
             ->second->FlushBuf
             .get_access<access::mode::read_write, access::target::host_buffer>(
                 cgh);
-    cgh.codeplay_host_task([=] {
+    cgh.host_task([=] {
       printf("%s", BufHostAcc.get_pointer());
       fflush(stdout);
     });

sycl/unittests/pi/cuda/test_interop_get_native.cpp

@@ -88,7 +88,7 @@ TEST_P(CudaInteropGetNativeTests, hostTaskGetNativeMem) {
   buffer<int, 1> syclBuffer(range<1>{1});
   syclQueue_->submit([&](handler &cgh) {
     auto syclAccessor = syclBuffer.get_access<access::mode::read>(cgh);
-    cgh.codeplay_host_task([=](interop_handle ih) {
+    cgh.host_task([=](interop_handle ih) {
       CUdeviceptr cudaPtr = ih.get_native_mem<backend::cuda>(syclAccessor);
       CUdeviceptr cudaPtrBase;
       size_t cudaPtrSize = 0;
@@ -106,7 +106,7 @@ TEST_P(CudaInteropGetNativeTests, hostTaskGetNativeMem) {
 TEST_P(CudaInteropGetNativeTests, hostTaskGetNativeQueue) {
   CUstream cudaStream = get_native<backend::cuda>(*syclQueue_);
   syclQueue_->submit([&](handler &cgh) {
-    cgh.codeplay_host_task([=](interop_handle ih) {
+    cgh.host_task([=](interop_handle ih) {
       CUstream cudaInteropStream = ih.get_native_queue<backend::cuda>();
       ASSERT_EQ(cudaInteropStream, cudaStream);
     });
@@ -116,7 +116,7 @@ TEST_P(CudaInteropGetNativeTests, hostTaskGetNativeQueue) {
 TEST_P(CudaInteropGetNativeTests, hostTaskGetNativeContext) {
   CUcontext cudaContext = get_native<backend::cuda>(syclQueue_->get_context());
   syclQueue_->submit([&](handler &cgh) {
-    cgh.codeplay_host_task([=](interop_handle ih) {
+    cgh.host_task([=](interop_handle ih) {
       CUcontext cudaInteropContext = ih.get_native_context<backend::cuda>();
       ASSERT_EQ(cudaInteropContext, cudaContext);
     });

sycl/unittests/scheduler/InOrderQueueHostTaskDeps.cpp

@@ -106,7 +106,7 @@ TEST_F(SchedulerTest, InOrderQueueHostTaskDeps) {
   InOrderQueue
       .submit([&](sycl::handler &CGH) {
         CGH.use_kernel_bundle(ExecBundle);
-        CGH.codeplay_host_task([=] {});
+        CGH.host_task([=] {});
       })
       .wait();