[DevASAN] Only report warning if passing host ptr to kernel (#16654)

UR Part: oneapi-src/unified-runtime#2569

---------

Co-authored-by: Kenneth Benzie (Benie) <[email protected]>

Author: 2 people

sycl/cmake/modules/UnifiedRuntimeTag.cmake

@@ -1,7 +1,7 @@
-# commit 9e48f543b8dd39d45563169433bb529583625dfe
-# Merge: 6a3fece6 1a1108b3
-# Author: Martin Grant <martin.morrisongrant@codeplay.com>
-# Date:   Wed Jan 15 14:33:29 2025 +0000
-#     Merge pull request #2540 from martygrant/martin/program-info-unswitch
-#     Move urProgramGetInfo success test from a switch to individual tests.
-set(UNIFIED_RUNTIME_TAG 9e48f543b8dd39d45563169433bb529583625dfe)
+# commit eaea885d5477c8936209175a5b00062ca44f5765
+# Merge: af4ab49c 2a03334c
+# Author: Kenneth Benzie (Benie) <k.benzie@codeplay.com>
+# Date:   Thu Jan 16 14:30:47 2025 +0000
+#     Merge pull request #2569 from zhaomaosu/asan-only-warn-host-ptr
+#     [DevASAN] Only report warning if passing host ptr to kernel
+set(UNIFIED_RUNTIME_TAG eaea885d5477c8936209175a5b00062ca44f5765)

sycl/test-e2e/AddressSanitizer/invalid-argument/host-pointer.cpp

@@ -1,29 +1,25 @@
 // REQUIRES: linux, cpu || (gpu && level_zero)
 // RUN: %{build} %device_asan_flags -O2 -g -o %t
-// RUN: env UR_LAYER_ASAN_OPTIONS="detect_kernel_arguments:1" %{run} %if gpu %{ not %} %t 2>&1 | FileCheck --check-prefixes %if cpu %{ CHECK-CPU %} %if gpu %{ CHECK-GPU %} %s
+// RUN: env UR_LAYER_ASAN_OPTIONS="detect_kernel_arguments:1" %{run} %t 2>&1 | FileCheck --check-prefixes %if cpu %{ CHECK-CPU %} %if gpu %{ CHECK-GPU %} %s
 
 #include <sycl/detail/core.hpp>
 #include <sycl/usm.hpp>
 
-///
-/// GPU devices don't support shared system USM currently, so passing host
-/// pointer to kernel is invalid.
-/// CPU devices support shared system USM.
-///
-
 int main() {
   sycl::queue Q;
+  auto *array = sycl::malloc_device<uintptr_t>(1, Q);
   auto hostPtr = new int;
 
   Q.submit([&](sycl::handler &h) {
-    h.single_task<class MyKernel>([=]() { *hostPtr = 0; });
+    h.single_task<class MyKernel>([=]() { array[0] = (uintptr_t)hostPtr; });
   });
   Q.wait();
 
   // CHECK-GPU: ERROR: DeviceSanitizer: invalid-argument
   // CHECK-GPU: The {{[0-9]+}}th argument {{.*}} is not a USM pointer
   // CHECK-CPU-NOT: ERROR: DeviceSanitizer: invalid-argument
 
+  sycl::free(array, Q);
   delete hostPtr;
   puts("PASS\n");
   return 0;