Merge branch 'sycl' into msan-always-reserve-origin-mem

zhaomaosu · zhaomaosu · commit 969e28473cc3 · 2025-09-04T03:48:27.000+02:00
diff --git a/libclc/CMakeLists.txt b/libclc/CMakeLists.txt
@@ -472,9 +472,11 @@ foreach( t ${LIBCLC_TARGETS_TO_BUILD} )
     elseif( ARCH STREQUAL nvptx OR ARCH STREQUAL nvptx64 )
       set( build_flags )
       set( opt_flags -O3 "--nvvm-reflect-enable=false" )
+      set( MACRO_ARCH ${ARCH} )
     elseif( ARCH STREQUAL amdgcn )
       set( build_flags )
       set( opt_flags -O3 --amdgpu-oclc-reflect-enable=false )
+      set( MACRO_ARCH ${ARCH} )
     else()
       set( build_flags )
       set( opt_flags -O3 )
diff --git a/sycl/source/detail/device_global_map.hpp b/sycl/source/detail/device_global_map.hpp
@@ -27,10 +27,17 @@ class DeviceGlobalMap {
   DeviceGlobalMap(bool OwnerControlledCleanup)
       : MOwnerControlledCleanup{OwnerControlledCleanup} {}
 
+  DeviceGlobalMap(const DeviceGlobalMap &) = delete;
+  DeviceGlobalMap &operator=(const DeviceGlobalMap &) = delete;
+
   ~DeviceGlobalMap() {
-    if (!MOwnerControlledCleanup)
-      for (auto &DeviceGlobalIt : MDeviceGlobals)
-        DeviceGlobalIt.second->cleanup();
+    try {
+      if (!MOwnerControlledCleanup)
+        for (auto &DeviceGlobalIt : MDeviceGlobals)
+          DeviceGlobalIt.second->cleanup();
+    } catch (std::exception &e) {
+      __SYCL_REPORT_EXCEPTION_TO_STREAM("exception in ~DeviceGlobalMap", e);
+    }
   }
 
   void initializeEntries(const RTDeviceBinaryImage *Img) {
diff --git a/sycl/source/detail/device_global_map_entry.hpp b/sycl/source/detail/device_global_map_entry.hpp
@@ -67,14 +67,14 @@ struct DeviceGlobalMapEntry {
   // Constructor for only initializing ID and pointer. The other members will
   // be initialized later.
   DeviceGlobalMapEntry(std::string UniqueId, const void *DeviceGlobalPtr)
-      : MUniqueId(UniqueId), MDeviceGlobalPtr(DeviceGlobalPtr) {}
+      : MUniqueId(std::move(UniqueId)), MDeviceGlobalPtr(DeviceGlobalPtr) {}
 
   // Constructor for only initializing ID, type size, and device image scope
   // flag. The pointer to the device global will be initialized later.
   DeviceGlobalMapEntry(std::string UniqueId, const RTDeviceBinaryImage *Img,
                        std::uint32_t DeviceGlobalTSize,
                        bool IsDeviceImageScopeDecorated)
-      : MUniqueId(UniqueId), MImages{Img},
+      : MUniqueId(std::move(UniqueId)), MImages{Img},
         MImageIdentifiers{reinterpret_cast<uintptr_t>(Img)},
         MDeviceGlobalTSize(DeviceGlobalTSize),
         MIsDeviceImageScopeDecorated(IsDeviceImageScopeDecorated) {}
diff --git a/sycl/source/detail/property_set_io.hpp b/sycl/source/detail/property_set_io.hpp
@@ -30,7 +30,7 @@ static IntT stringViewToInt(const std::string_view &SV) {
   if (SV.empty())
     return Result;
 
-  bool Negate = std::is_signed_v<IntT> && SV[0] == '-';
+  const bool Negate = std::is_signed_v<IntT> && SV[0] == '-';
 
   for (size_t I = static_cast<size_t>(Negate); I < SV.size(); ++I) {
     const char CurrentC = SV[I];
diff --git a/sycl/test-e2e/Graph/Explicit/buffer_copy_host2target.cpp b/sycl/test-e2e/Graph/Explicit/buffer_copy_host2target.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Host to device copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Host to device copy command not supported for OpenCL
 
 #define GRAPH_E2E_EXPLICIT
 
diff --git a/sycl/test-e2e/Graph/Explicit/buffer_copy_host2target_2d.cpp b/sycl/test-e2e/Graph/Explicit/buffer_copy_host2target_2d.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Host to device copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Host to device copy command not supported for OpenCL
 
 #define GRAPH_E2E_EXPLICIT
 
diff --git a/sycl/test-e2e/Graph/Explicit/buffer_copy_host2target_offset.cpp b/sycl/test-e2e/Graph/Explicit/buffer_copy_host2target_offset.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Host to device copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Host to device copy command not supported for OpenCL
 
 #define GRAPH_E2E_EXPLICIT
 
diff --git a/sycl/test-e2e/Graph/Explicit/buffer_copy_target2host.cpp b/sycl/test-e2e/Graph/Explicit/buffer_copy_target2host.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Device to host copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Device to host copy command not supported for OpenCL
 
 #define GRAPH_E2E_EXPLICIT
 
diff --git a/sycl/test-e2e/Graph/Explicit/buffer_copy_target2host_2d.cpp b/sycl/test-e2e/Graph/Explicit/buffer_copy_target2host_2d.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Device to host copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Device to host copy command not supported for OpenCL
 
 #define GRAPH_E2E_EXPLICIT
 
diff --git a/sycl/test-e2e/Graph/Explicit/buffer_copy_target2host_offset.cpp b/sycl/test-e2e/Graph/Explicit/buffer_copy_target2host_offset.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Device to host copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Device to host copy command not supported for OpenCL
 
 #define GRAPH_E2E_EXPLICIT
 
diff --git a/sycl/test-e2e/Graph/Explicit/host_task2_multiple_roots.cpp b/sycl/test-e2e/Graph/Explicit/host_task2_multiple_roots.cpp
@@ -5,9 +5,9 @@
 
 // REQUIRES: aspect-usm_shared_allocations
 
-// Intended - Concurrent access to shared USM allocations is not supported by
-// CUDA on Windows
 // UNSUPPORTED: cuda && windows
+// UNSUPPORTED-INTENDED: Concurrent access to shared USM allocations is not
+// supported by CUDA on Windows
 
 // Test is flaky on Windows for all targets, disable until it can be fixed
 // UNSUPPORTED: windows
diff --git a/sycl/test-e2e/Graph/Explicit/host_task_multiple_roots.cpp b/sycl/test-e2e/Graph/Explicit/host_task_multiple_roots.cpp
@@ -5,9 +5,9 @@
 
 // REQUIRES: aspect-usm_shared_allocations
 
-// Intended Concurrent access to shared USM allocations is not supported by
-// CUDA on Windows
 // UNSUPPORTED: cuda && windows
+// UNSUPPORTED-INTENDED: Concurrent access to shared USM allocations is not
+// supported by CUDA on Windows
 
 // Test is flaky on Windows for all targets, disable until it can be fixed
 // UNSUPPORTED: windows
diff --git a/sycl/test-e2e/Graph/Explicit/memadvise.cpp b/sycl/test-e2e/Graph/Explicit/memadvise.cpp
@@ -3,8 +3,8 @@
 
 // REQUIRES: aspect-usm_shared_allocations
 
-// Intended - Mem advise command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Mem advise command not supported for OpenCL
 
 // Since Mem advise is only a memory hint that doesn't
 // impact results but only performances, we verify
diff --git a/sycl/test-e2e/Graph/Explicit/prefetch.cpp b/sycl/test-e2e/Graph/Explicit/prefetch.cpp
@@ -3,8 +3,8 @@
 
 // REQUIRES: aspect-usm_shared_allocations
 
-// Intended - prefetch command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: prefetch command not supported for OpenCL
 
 // Since Prefetch is only a memory hint that doesn't
 // impact results but only performances, we verify
diff --git a/sycl/test-e2e/Graph/Explicit/spec_constants_kernel_bundle_api.cpp b/sycl/test-e2e/Graph/Explicit/spec_constants_kernel_bundle_api.cpp
@@ -4,9 +4,10 @@
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
 
-// Intended - The following limitation is not restricted to Sycl-Graph
-// but comes from the orignal test : `SpecConstants/2020/kernel-bundle-api.cpp`
 // UNSUPPORTED: hip
+// UNSUPPORTED-INTENDED: The following limitation is not restricted to
+// Sycl-Graph but comes from the orignal test :
+// `SpecConstants/2020/kernel-bundle-api.cpp`
 
 #define GRAPH_E2E_EXPLICIT
 
diff --git a/sycl/test-e2e/Graph/Explicit/work_group_size_prop.cpp b/sycl/test-e2e/Graph/Explicit/work_group_size_prop.cpp
@@ -4,12 +4,12 @@
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
 
-// Intended OpenCL fail due to backend:
+// UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: OpenCL fail due to backend:
 // The OpenCL emulation layer does not return `CL_INVALID_WORK_GROUP_SIZE` as it
 // should. So the Sycl graph support cannot correctly catch the error and throw
 // the appropriate exception for negative test. An issue has been reported
 // https://github.com/bashbaug/SimpleOpenCLSamples/issues/95
-// UNSUPPORTED: opencl
 
 #define GRAPH_E2E_EXPLICIT
 
diff --git a/sycl/test-e2e/Graph/RecordReplay/buffer_copy_host2target.cpp b/sycl/test-e2e/Graph/RecordReplay/buffer_copy_host2target.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Host to device copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Host to device copy command not supported for OpenCL
 
 #define GRAPH_E2E_RECORD_REPLAY
 
diff --git a/sycl/test-e2e/Graph/RecordReplay/buffer_copy_host2target_2d.cpp b/sycl/test-e2e/Graph/RecordReplay/buffer_copy_host2target_2d.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Host to device copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Host to device copy command not supported for OpenCL
 
 #define GRAPH_E2E_RECORD_REPLAY
 
diff --git a/sycl/test-e2e/Graph/RecordReplay/buffer_copy_host2target_offset.cpp b/sycl/test-e2e/Graph/RecordReplay/buffer_copy_host2target_offset.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Host to device copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Host to device copy command not supported for OpenCL
 
 #define GRAPH_E2E_RECORD_REPLAY
 
diff --git a/sycl/test-e2e/Graph/RecordReplay/buffer_copy_target2host.cpp b/sycl/test-e2e/Graph/RecordReplay/buffer_copy_target2host.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Device to host copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Device to host copy command not supported for OpenCL
 
 #define GRAPH_E2E_RECORD_REPLAY
 
diff --git a/sycl/test-e2e/Graph/RecordReplay/buffer_copy_target2host_2d.cpp b/sycl/test-e2e/Graph/RecordReplay/buffer_copy_target2host_2d.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Device to host copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Device to host copy command not supported for OpenCL
 
 #define GRAPH_E2E_RECORD_REPLAY
 
diff --git a/sycl/test-e2e/Graph/RecordReplay/buffer_copy_target2host_offset.cpp b/sycl/test-e2e/Graph/RecordReplay/buffer_copy_target2host_offset.cpp
@@ -3,8 +3,8 @@
 // Extra run to check for leaks in Level Zero using UR_L0_LEAKS_DEBUG
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
-// Intended - Device to host copy command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Device to host copy command not supported for OpenCL
 
 #define GRAPH_E2E_RECORD_REPLAY
 
diff --git a/sycl/test-e2e/Graph/RecordReplay/host_task2_multiple_roots.cpp b/sycl/test-e2e/Graph/RecordReplay/host_task2_multiple_roots.cpp
@@ -5,9 +5,9 @@
 
 // REQUIRES: aspect-usm_shared_allocations
 
-// Intended - Concurrent access to shared USM allocations is not supported by
-// CUDA on Windows
 // UNSUPPORTED: cuda && windows
+// UNSUPPORTED-INTENDED: Concurrent access to shared USM allocations is not
+// supported by CUDA on Windows
 
 // Test is flaky on Windows for all targets, disable until it can be fixed
 // UNSUPPORTED: windows
diff --git a/sycl/test-e2e/Graph/RecordReplay/host_task_multiple_roots.cpp b/sycl/test-e2e/Graph/RecordReplay/host_task_multiple_roots.cpp
@@ -5,9 +5,9 @@
 
 // REQUIRES: aspect-usm_shared_allocations
 
-// Concurrent access to shared USM allocations is not supported by
-// CUDA on Windows
 // UNSUPPORTED: cuda && windows
+// UNSUPPORTED-INTENDED: Concurrent access to shared USM allocations is not
+// supported by CUDA on Windows
 
 // Test is flaky on Windows for all targets, disable until it can be fixed
 // UNSUPPORTED: windows
diff --git a/sycl/test-e2e/Graph/RecordReplay/memadvise.cpp b/sycl/test-e2e/Graph/RecordReplay/memadvise.cpp
@@ -3,8 +3,8 @@
 
 // REQUIRES: aspect-usm_shared_allocations
 
-// Intended - Mem advise command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: Mem advise command not supported for OpenCL
 
 // Since Mem advise is only a memory hint that doesn't
 // impact results but only performances, we verify
diff --git a/sycl/test-e2e/Graph/RecordReplay/prefetch.cpp b/sycl/test-e2e/Graph/RecordReplay/prefetch.cpp
@@ -3,8 +3,8 @@
 
 // REQUIRES: aspect-usm_shared_allocations
 
-// Inteded - prefetch command not supported for OpenCL
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: prefetch command not supported for OpenCL
 
 // Since Prefetch is only a memory hint that doesn't
 // impact results but only performances, we verify
diff --git a/sycl/test-e2e/Graph/RecordReplay/spec_constants_kernel_bundle_api.cpp b/sycl/test-e2e/Graph/RecordReplay/spec_constants_kernel_bundle_api.cpp
@@ -4,9 +4,10 @@
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
 
-// Intended - The following limitation is not restricted to Sycl-Graph
-// but comes from the orignal test : `SpecConstants/2020/kernel-bundle-api.cpp`
 // UNSUPPORTED: hip
+// UNSUPPORTED-INTENDED: The following limitation is not restricted to
+// Sycl-Graph but comes from the orignal test :
+// `SpecConstants/2020/kernel-bundle-api.cpp`
 
 #define GRAPH_E2E_RECORD_REPLAY
 
diff --git a/sycl/test-e2e/Graph/RecordReplay/work_group_size_prop.cpp b/sycl/test-e2e/Graph/RecordReplay/work_group_size_prop.cpp
@@ -4,12 +4,12 @@
 // RUN: %if level_zero %{%{l0_leak_check} %{run} %t.out 2>&1 | FileCheck %s --implicit-check-not=LEAK %}
 //
 //
-// Intended - OpenCL fail due to backend
+// UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: OpenCL fail due to backend
 // The OpenCL emulation layer does not return `CL_INVALID_WORK_GROUP_SIZE` as it
 // should. So the Sycl graph support cannot correctly catch the error and throw
 // the approriate exception for negative test. An issue has been reported
 // https://github.com/bashbaug/SimpleOpenCLSamples/issues/95
-// UNSUPPORTED: opencl
 
 #define GRAPH_E2E_RECORD_REPLAY
 
diff --git a/sycl/test-e2e/Graph/UnsupportedDevice/device_query.cpp b/sycl/test-e2e/Graph/UnsupportedDevice/device_query.cpp
@@ -1,8 +1,8 @@
 // RUN: %{build} -o %t.out
 // RUN: %{run} %t.out
 
-// Intended - OpenCL support depends on extensions
 // UNSUPPORTED: opencl
+// UNSUPPORTED-INTENDED: OpenCL support depends on extensions
 
 // Tests the using device query for graphs support, and that the return value
 // matches expectations.
diff --git a/sycl/test-e2e/HostInteropTask/host-task-two-queues.cpp b/sycl/test-e2e/HostInteropTask/host-task-two-queues.cpp
@@ -5,45 +5,48 @@
 #include <sycl/detail/core.hpp>
 #include <vector>
 
-namespace S = sycl;
-
 #define WIDTH 5
 #define HEIGHT 5
 
 void test() {
-  auto EH = [](S::exception_list EL) {
+  auto EH = [](sycl::exception_list EL) {
     for (const std::exception_ptr &E : EL) {
       throw E;
     }
   };
 
-  S::queue Q1(EH);
-  S::queue Q2(EH);
+  sycl::queue Q1(EH);
+  sycl::queue Q2(EH);
 
   std::vector<int> DataA(WIDTH * HEIGHT, 2);
   std::vector<int> DataB(WIDTH * HEIGHT, 3);
   std::vector<int> DataC(WIDTH * HEIGHT, 1);
 
-  S::buffer<int, 2> BufA{DataA.data(), S::range<2>{WIDTH, HEIGHT}};
-  S::buffer<int, 2> BufB{DataB.data(), S::range<2>{WIDTH, HEIGHT}};
-  S::buffer<int, 2> BufC{DataC.data(), S::range<2>{WIDTH, HEIGHT}};
+  sycl::buffer<int, 2> BufA{DataA.data(), sycl::range<2>{WIDTH, HEIGHT}};
+  sycl::buffer<int, 2> BufB{DataB.data(), sycl::range<2>{WIDTH, HEIGHT}};
+  sycl::buffer<int, 2> BufC{DataC.data(), sycl::range<2>{WIDTH, HEIGHT}};
 
-  auto CG1 = [&](S::handler &CGH) {
-    auto AccA = BufA.get_access<S::access::mode::read>(CGH);
-    auto AccB = BufB.get_access<S::access::mode::read>(CGH);
-    auto AccC = BufC.get_access<S::access::mode::read_write>(CGH);
-    auto Kernel = [=](S::nd_item<2> Item) {
+  auto CG1 = [&](sycl::handler &CGH) {
+    auto AccA = BufA.get_access<sycl::access_mode::read>(CGH);
+    auto AccB = BufB.get_access<sycl::access_mode::read>(CGH);
+    auto AccC = BufC.get_access<sycl::access_mode::read_write>(CGH);
+    auto Kernel = [=](sycl::nd_item<2> Item) {
       size_t W = Item.get_global_id(0);
       size_t H = Item.get_global_id(1);
       AccC[W][H] += AccA[W][H] * AccB[W][H];
     };
-    CGH.parallel_for<class K1>(S::nd_range<2>({WIDTH, HEIGHT}, {1, 1}), Kernel);
+    CGH.parallel_for<class K1>(sycl::nd_range<2>({WIDTH, HEIGHT}, {1, 1}),
+                               Kernel);
   };
 
-  auto CG2 = [&](S::handler &CGH) {
-    auto AccA = BufA.get_access<sycl::access::mode::read>(CGH);
-    auto AccB = BufB.get_access<sycl::access::mode::read>(CGH);
-    auto AccC = BufC.get_access<sycl::access::mode::read_write>(CGH);
+  auto CG2 = [&](sycl::handler &CGH) {
+    auto AccA =
+        BufA.get_access<sycl::access_mode::read, sycl::target::host_task>(CGH);
+    auto AccB =
+        BufB.get_access<sycl::access_mode::read, sycl::target::host_task>(CGH);
+    auto AccC =
+        BufC.get_access<sycl::access_mode::read_write, sycl::target::host_task>(
+            CGH);
 
     CGH.host_task([=] {
       for (size_t I = 0; I < WIDTH; ++I)
diff --git a/sycl/test-e2e/Regression/commandlist/Inputs/main.cpp b/sycl/test-e2e/Regression/commandlist/Inputs/main.cpp
diff --git a/sycl/test-e2e/bindless_images/copies/host_to_host_pitched.cpp b/sycl/test-e2e/bindless_images/copies/host_to_host_pitched.cpp
diff --git a/sycl/test-e2e/bindless_images/sampling_2D_USM_host.cpp b/sycl/test-e2e/bindless_images/sampling_2D_USM_host.cpp
diff --git a/sycl/test-e2e/lit.cfg.py b/sycl/test-e2e/lit.cfg.py
diff --git a/sycl/test/e2e_test_requirements/no-unsupported-without-info.cpp b/sycl/test/e2e_test_requirements/no-unsupported-without-info.cpp
diff --git a/unified-runtime/source/adapters/level_zero/device.cpp b/unified-runtime/source/adapters/level_zero/device.cpp
diff --git a/unified-runtime/source/adapters/level_zero/device.hpp b/unified-runtime/source/adapters/level_zero/device.hpp
diff --git a/xpti/include/xpti/xpti_trace_framework.hpp b/xpti/include/xpti/xpti_trace_framework.hpp
diff --git a/xptifw/src/CMakeLists.txt b/xptifw/src/CMakeLists.txt
