diff --git a/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-host.cpp b/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-host.cpp index 8f8a91ec56e5e..98299d84a3f11 100644 --- a/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-host.cpp +++ b/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-host.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t // RUN: %force_device_asan_rt %{run} not %t 2>&1 | FileCheck %s #include diff --git a/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-minus1.cpp b/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-minus1.cpp index 9503ef4bb5af4..ba49fdb789cf7 100644 --- a/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-minus1.cpp +++ b/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-minus1.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %force_device_asan_rt %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_HOST -O0 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-plus1.cpp b/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-plus1.cpp index 17efe090d4cc5..55c776d017df6 100644 --- a/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-plus1.cpp +++ b/sycl/test-e2e/AddressSanitizer/bad-free/bad-free-plus1.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %force_device_asan_rt %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_HOST -O0 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/common/demangle-kernel-name.cpp b/sycl/test-e2e/AddressSanitizer/common/demangle-kernel-name.cpp index 7c8cb8d3569f5..45951b1ab2734 100644 --- a/sycl/test-e2e/AddressSanitizer/common/demangle-kernel-name.cpp +++ b/sycl/test-e2e/AddressSanitizer/common/demangle-kernel-name.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -o %t // RUN: %{run} not %t &> %t.txt ; FileCheck --input-file %t.txt %s #include diff --git a/sycl/test-e2e/AddressSanitizer/common/kernel-debug.cpp b/sycl/test-e2e/AddressSanitizer/common/options-debug.cpp similarity index 84% rename from sycl/test-e2e/AddressSanitizer/common/kernel-debug.cpp rename to sycl/test-e2e/AddressSanitizer/common/options-debug.cpp index 9d3361a239fe1..2e9bc8bb623f6 100644 --- a/sycl/test-e2e/AddressSanitizer/common/kernel-debug.cpp +++ b/sycl/test-e2e/AddressSanitizer/common/options-debug.cpp @@ -1,6 +1,5 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -o %t -// RUN: env UR_LAYER_ASAN_OPTIONS=debug:1 %{run} %t 2>&1 | FileCheck --check-prefixes CHECK-DEBUG %s // RUN: env UR_LAYER_ASAN_OPTIONS=debug:0 %{run} %t 2>&1 | FileCheck %s #include @@ -23,7 +22,6 @@ int main() { }); }); Q.wait(); - // CHECK-DEBUG: [kernel] // CHECK-NOT: [kernel] sycl::free(array, Q); diff --git a/sycl/test-e2e/AddressSanitizer/common/options-invalid.cpp b/sycl/test-e2e/AddressSanitizer/common/options-invalid-values.cpp similarity index 95% rename from sycl/test-e2e/AddressSanitizer/common/options-invalid.cpp rename to sycl/test-e2e/AddressSanitizer/common/options-invalid-values.cpp index a6e3ef21d0567..bedf953e80e8e 100644 --- a/sycl/test-e2e/AddressSanitizer/common/options-invalid.cpp +++ b/sycl/test-e2e/AddressSanitizer/common/options-invalid-values.cpp @@ -1,7 +1,8 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t // RUN: %{run} %t +// clang-format off // Invalid ur option format // RUN: env UR_LAYER_ASAN_OPTIONS=a:1,b:1 %{run} not %t 2>&1 | FileCheck %s --check-prefixes INVALID-FORMAT // INVALID-FORMAT: [ERROR]: Wrong format of the UR_LAYER_ASAN_OPTIONS environment variable value @@ -20,8 +21,7 @@ // INVALID-REDZONE: [ERROR]: "redzone" should be an integer in range[0, 16]. // RUN: env UR_LAYER_ASAN_OPTIONS=max_redzone:abc %{run} not %t 2>&1 | FileCheck %s --check-prefixes INVALID-MAXREDZONE // INVALID-MAXREDZONE: [ERROR]: "max_redzone" should be an integer in range[0, 2048]. - - +// clang-format on #include diff --git a/sycl/test-e2e/AddressSanitizer/common/option-redzone-size.cpp b/sycl/test-e2e/AddressSanitizer/common/options-redzone.cpp similarity index 88% rename from sycl/test-e2e/AddressSanitizer/common/option-redzone-size.cpp rename to sycl/test-e2e/AddressSanitizer/common/options-redzone.cpp index ac0cadf31b5a7..8f96415587572 100644 --- a/sycl/test-e2e/AddressSanitizer/common/option-redzone-size.cpp +++ b/sycl/test-e2e/AddressSanitizer/common/options-redzone.cpp @@ -1,9 +1,12 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -DUNSAFE -O0 -g -o %t1.out // RUN: env UR_LAYER_ASAN_OPTIONS=redzone:64 %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -DSAFE -O0 -g -o %t2.out + +// clang-format off // RUN: env UR_LOG_SANITIZER=level:debug UR_LAYER_ASAN_OPTIONS=redzone:8 %{run} %t2.out 2>&1 | FileCheck --check-prefixes CHECK-MIN %s // RUN: env UR_LOG_SANITIZER=level:debug UR_LAYER_ASAN_OPTIONS=max_redzone:4096 %{run} %t2.out 2>&1 | FileCheck --check-prefixes CHECK-MAX %s +// clang-format on #include @@ -21,7 +24,7 @@ int main() { }).wait(); // CHECK: ERROR: DeviceSanitizer: out-of-bounds-access on Device USM // CHECK: {{READ of size 1 at kernel <.*Test> LID\(0, 0, 0\) GID\(0, 0, 0\)}} - // CHECK: {{ #0 .* .*option-redzone-size.cpp:}}[[@LINE-7]] + // CHECK: {{ #0 .* .*options-redzone.cpp:}}[[@LINE-7]] // CHECK-MIN: Trying to set redzone size to a value less than 16 is ignored // CHECK-MAX: Trying to set max redzone size to a value greater than 2048 is ignored diff --git a/sycl/test-e2e/AddressSanitizer/common/statistics.cpp b/sycl/test-e2e/AddressSanitizer/common/options-statistics.cpp similarity index 95% rename from sycl/test-e2e/AddressSanitizer/common/statistics.cpp rename to sycl/test-e2e/AddressSanitizer/common/options-statistics.cpp index 07bdb734738ee..a36c5bbf1a5be 100644 --- a/sycl/test-e2e/AddressSanitizer/common/statistics.cpp +++ b/sycl/test-e2e/AddressSanitizer/common/options-statistics.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -o %t // RUN: %{run} %t 2>&1 | FileCheck %s // RUN: env UR_LAYER_ASAN_OPTIONS=print_stats:1 %{run} %t 2>&1 | FileCheck --check-prefixes CHECK-STATS %s diff --git a/sycl/test-e2e/AddressSanitizer/double-free/double-free.cpp b/sycl/test-e2e/AddressSanitizer/double-free/double-free.cpp index c0e31d5336614..61137c15c0ec7 100644 --- a/sycl/test-e2e/AddressSanitizer/double-free/double-free.cpp +++ b/sycl/test-e2e/AddressSanitizer/double-free/double-free.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %force_device_asan_rt UR_LAYER_ASAN_OPTIONS="quarantine_size_mb:1;detect_kernel_arguments:0" %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_HOST -O0 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/invalid-argument/bad-context.cpp b/sycl/test-e2e/AddressSanitizer/invalid-argument/bad-context.cpp index ee92cb4f2f34c..d74ba81f297fe 100644 --- a/sycl/test-e2e/AddressSanitizer/invalid-argument/bad-context.cpp +++ b/sycl/test-e2e/AddressSanitizer/invalid-argument/bad-context.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux, (gpu && level_zero), cpu +// REQUIRES: linux, cpu && (gpu && level_zero) // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O2 -g -o %t // RUN: env SYCL_PREFER_UR=1 UR_LAYER_ASAN_OPTIONS="detect_kernel_arguments:1" %{run} not %t 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s diff --git a/sycl/test-e2e/AddressSanitizer/invalid-argument/host-pointer.cpp b/sycl/test-e2e/AddressSanitizer/invalid-argument/host-pointer.cpp index bfebfd4288bfe..a12a9570076bc 100644 --- a/sycl/test-e2e/AddressSanitizer/invalid-argument/host-pointer.cpp +++ b/sycl/test-e2e/AddressSanitizer/invalid-argument/host-pointer.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux, cpu || level_zero +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -o %t // RUN: env SYCL_PREFER_UR=1 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 diff --git a/sycl/test-e2e/AddressSanitizer/invalid-argument/out-of-bounds.cpp b/sycl/test-e2e/AddressSanitizer/invalid-argument/out-of-bounds.cpp index 4973cdeddab0d..b6e2fa9ccbc0e 100644 --- a/sycl/test-e2e/AddressSanitizer/invalid-argument/out-of-bounds.cpp +++ b/sycl/test-e2e/AddressSanitizer/invalid-argument/out-of-bounds.cpp @@ -1,5 +1,4 @@ -// REQUIRES: linux, gpu - +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -o %t // RUN: env SYCL_PREFER_UR=1 UR_LAYER_ASAN_OPTIONS="detect_kernel_arguments:1" %{run} not %t 2>&1 | FileCheck %s diff --git a/sycl/test-e2e/AddressSanitizer/invalid-argument/released-pointer.cpp b/sycl/test-e2e/AddressSanitizer/invalid-argument/released-pointer.cpp index 3c8d32bbd68e0..f67a3b23019b0 100644 --- a/sycl/test-e2e/AddressSanitizer/invalid-argument/released-pointer.cpp +++ b/sycl/test-e2e/AddressSanitizer/invalid-argument/released-pointer.cpp @@ -1,5 +1,4 @@ -// REQUIRES: linux, gpu - +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -o %t // RUN: env SYCL_PREFER_UR=1 UR_LAYER_ASAN_OPTIONS="quarantine_size_mb:1;detect_kernel_arguments:1" %{run} not %t 2>&1 | FileCheck %s diff --git a/sycl/test-e2e/AddressSanitizer/lit.local.cfg b/sycl/test-e2e/AddressSanitizer/lit.local.cfg index 8c0087f665dc6..e7575dcca0e13 100644 --- a/sycl/test-e2e/AddressSanitizer/lit.local.cfg +++ b/sycl/test-e2e/AddressSanitizer/lit.local.cfg @@ -10,9 +10,5 @@ config.substitutions.append( config.unsupported_features += ['cuda', 'hip'] -# FIXME: Skip some of gpu devices, waiting for gfx driver uplifting -config.unsupported_features += ['gpu-intel-gen9', 'gpu-intel-gen11', 'gpu-intel-gen12', 'gpu-intel-pvc'] - -# GPU testing requires level_zero -if 'opencl:gpu' in config.sycl_devices: - config.required_features += ['level_zero'] +# https://github.com/intel/llvm/issues/15953 +config.unsupported_features += ['gpu-intel-gen12'] diff --git a/sycl/test-e2e/AddressSanitizer/memory-leak/memory-leak.cpp b/sycl/test-e2e/AddressSanitizer/memory-leak/memory-leak.cpp index 8fe5e431e6eec..fde2fb62f3874 100644 --- a/sycl/test-e2e/AddressSanitizer/memory-leak/memory-leak.cpp +++ b/sycl/test-e2e/AddressSanitizer/memory-leak/memory-leak.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux, cpu +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t // RUN: %{run} %t 2>&1 | FileCheck %s diff --git a/sycl/test-e2e/AddressSanitizer/misaligned/misalign-int.cpp b/sycl/test-e2e/AddressSanitizer/misaligned/misalign-int.cpp index 9fac7f0f744c4..cd771a86cc2a1 100644 --- a/sycl/test-e2e/AddressSanitizer/misaligned/misalign-int.cpp +++ b/sycl/test-e2e/AddressSanitizer/misaligned/misalign-int.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: env SYCL_PREFER_UR=1 %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/misaligned/misalign-long.cpp b/sycl/test-e2e/AddressSanitizer/misaligned/misalign-long.cpp index 668fb413849a9..9600442bd88fc 100644 --- a/sycl/test-e2e/AddressSanitizer/misaligned/misalign-long.cpp +++ b/sycl/test-e2e/AddressSanitizer/misaligned/misalign-long.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: env SYCL_PREFER_UR=1 %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/misaligned/misalign-short.cpp b/sycl/test-e2e/AddressSanitizer/misaligned/misalign-short.cpp index e3b5565036fa1..f65c5e9826dfc 100644 --- a/sycl/test-e2e/AddressSanitizer/misaligned/misalign-short.cpp +++ b/sycl/test-e2e/AddressSanitizer/misaligned/misalign-short.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: env SYCL_PREFER_UR=1 %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/multiple-reports/multiple_kernels.cpp b/sycl/test-e2e/AddressSanitizer/multiple-reports/multiple_kernels.cpp index 1228dd94fde9a..087ecb8684458 100644 --- a/sycl/test-e2e/AddressSanitizer/multiple-reports/multiple_kernels.cpp +++ b/sycl/test-e2e/AddressSanitizer/multiple-reports/multiple_kernels.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -Xarch_device -fsanitize-recover=address -O2 -g -o %t // RUN: env SYCL_PREFER_UR=1 %{run} %t 2>&1 | FileCheck %s diff --git a/sycl/test-e2e/AddressSanitizer/multiple-reports/one_kernel.cpp b/sycl/test-e2e/AddressSanitizer/multiple-reports/one_kernel.cpp index 9e845b429b42a..0aeb6fd661808 100644 --- a/sycl/test-e2e/AddressSanitizer/multiple-reports/one_kernel.cpp +++ b/sycl/test-e2e/AddressSanitizer/multiple-reports/one_kernel.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -Xarch_device -fsanitize-recover=address -O2 -g -o %t // RUN: env SYCL_PREFER_UR=1 %{run} %t 2>&1 | FileCheck %s diff --git a/sycl/test-e2e/AddressSanitizer/nullpointer/global_nullptr.cpp b/sycl/test-e2e/AddressSanitizer/nullpointer/global_nullptr.cpp index d712dcdeeb1ef..4b7250620f1d1 100644 --- a/sycl/test-e2e/AddressSanitizer/nullpointer/global_nullptr.cpp +++ b/sycl/test-e2e/AddressSanitizer/nullpointer/global_nullptr.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/nullpointer/private_nullptr.cpp b/sycl/test-e2e/AddressSanitizer/nullpointer/private_nullptr.cpp index 6b013a2aee1e2..27b4b5a6fab17 100644 --- a/sycl/test-e2e/AddressSanitizer/nullpointer/private_nullptr.cpp +++ b/sycl/test-e2e/AddressSanitizer/nullpointer/private_nullptr.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out @@ -22,8 +22,7 @@ int main() { sycl::nd_range<1>(N, 1), [=](sycl::nd_item<1> item) { auto private_array = sycl::ext::oneapi::experimental::static_address_cast< - sycl::access::address_space::private_space, - sycl::access::decorated::no>(array); + sycl::access::address_space::private_space>(array); private_array[0] = 0; }); Q.wait(); diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global.cpp index 32a25f35db91d..36c66562c08f4 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global_image_scope.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global_image_scope.cpp index 5c88e8e792fc8..b4033f7cad4cb 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global_image_scope.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global_image_scope.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global_image_scope_unaligned.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global_image_scope_unaligned.cpp index cfc41be7db479..2b6914d9818ee 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global_image_scope_unaligned.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/device_global_image_scope_unaligned.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/multi_device_images.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/multi_device_images.cpp index 914b80a89521f..5cab931adc4ab 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/multi_device_images.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/DeviceGlobal/multi_device_images.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -DUSER_CODE_1 -c -o %t1.o // RUN: %{build} %device_asan_flags -O2 -g -DUSER_CODE_2 -c -o %t2.o // RUN: %clangxx -fsycl %device_asan_flags -O2 -g %t1.o %t2.o -o %t.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/large_group_size.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/large_group_size.cpp index 86ea99bd14359..2627e1830fa77 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/large_group_size.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/large_group_size.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -o %t // RUN: env SYCL_PREFER_UR=1 %{run} not %t 2>&1 | FileCheck --check-prefixes CHECK %s diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_char.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_char.cpp index 1173d76f71a5d..c9451aca29c48 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_char.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_char.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_double.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_double.cpp index 68913ea479af0..2ccc1580e48d1 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_double.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_double.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux, aspect-fp64 +// REQUIRES: linux, cpu || (gpu && level_zero), aspect-fp64 // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_func.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_func.cpp index 6cc9835d092db..772493776f15f 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_func.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_func.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_int.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_int.cpp index 676b59fc4e17d..7f5682f031ceb 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_int.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_int.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_short.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_short.cpp index 32a094fa966ac..654cb1a662bb9 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_short.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_for_short.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_no_local_size.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_no_local_size.cpp index 06df087fd0915..cd20a7ae381b4 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_no_local_size.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/parallel_no_local_size.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O0 -g -o %t1.out // RUN: env SYCL_PREFER_UR=1 %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK-DEVICE %s // RUN: %{build} %device_asan_flags -DMALLOC_DEVICE -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/unaligned_shadow_memory.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/unaligned_shadow_memory.cpp index 16c5e471c365d..5d6f666216c59 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/unaligned_shadow_memory.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/USM/unaligned_shadow_memory.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -DTEST1 -O0 -g -o %t1.out // RUN: env SYCL_PREFER_UR=1 %{run} not %t1.out 2>&1 | FileCheck --check-prefixes CHECK,CHECK1 %s // RUN: %{build} %device_asan_flags -DTEST2 -O0 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer.cpp index 76f0a101c8ea3..6dfa41c0501fe 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_2d.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_2d.cpp index 13adf2fb16d1b..51cef0e06d71b 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_2d.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_2d.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_3d.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_3d.cpp index c497b64cad4b9..b01599e43cf88 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_3d.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_3d.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_copy_fill.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_copy_fill.cpp index ac50c0f00b836..13f7d5f74943b 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_copy_fill.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/buffer_copy_fill.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/subbuffer.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/subbuffer.cpp index b873b2c83216f..6bd5566aef3d4 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/subbuffer.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/buffer/subbuffer.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/group_local_memory.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/group_local_memory.cpp index 0d18a06ba3945..7355d1f98bd70 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/group_local_memory.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/group_local_memory.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -g -O0 -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -g -O1 -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_basic.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_basic.cpp index 2357300b685ba..590a2d0c88843 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_basic.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_basic.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -g -O0 -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -g -O1 -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_function.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_function.cpp index 46f3e9093ba9e..43d8fb4e07bdf 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_function.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_function.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -g -O0 -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -g -O1 -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_multiargs.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_multiargs.cpp index 2ae9408523a67..412159fbd41c9 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_multiargs.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/local_accessor_multiargs.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -g -O0 -o %t1.out // RUN: %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -g -O1 -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/multiple_source.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/multiple_source.cpp index aab9beab711a4..abb152ab4719a 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/multiple_source.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/local/multiple_source.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O2 -g -DUSER_CODE_1 -c -o %t1.o // RUN: %{build} %device_asan_flags -O2 -g -DUSER_CODE_2 -c -o %t2.o // RUN: %clangxx -fsycl %device_asan_flags -O2 -g %t1.o %t2.o -o %t.out diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/private/multiple_private.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/private/multiple_private.cpp index ec2a0b3fb435a..b2ff0c500b13a 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/private/multiple_private.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/private/multiple_private.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} -Wno-error=array-bounds %device_asan_flags -DVAR=1 -O2 -g -o %t1 // RUN: env SYCL_PREFER_UR=1 %{run} not %t1 2>&1 | FileCheck --check-prefixes CHECK,CHECK-VAR1 %s // RUN: %{build} -Wno-error=array-bounds %device_asan_flags -DVAR=2 -O2 -g -o %t2 diff --git a/sycl/test-e2e/AddressSanitizer/out-of-bounds/private/single_private.cpp b/sycl/test-e2e/AddressSanitizer/out-of-bounds/private/single_private.cpp index 5743c1d03d0e2..50480112367f3 100644 --- a/sycl/test-e2e/AddressSanitizer/out-of-bounds/private/single_private.cpp +++ b/sycl/test-e2e/AddressSanitizer/out-of-bounds/private/single_private.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t1.out // RUN: env SYCL_PREFER_UR=1 %{run} not %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_asan_flags -O1 -g -o %t2.out diff --git a/sycl/test-e2e/AddressSanitizer/use-after-free/quarantine-free.cpp b/sycl/test-e2e/AddressSanitizer/use-after-free/quarantine-free.cpp index 1a8a9d15666ad..aa36fec854af3 100644 --- a/sycl/test-e2e/AddressSanitizer/use-after-free/quarantine-free.cpp +++ b/sycl/test-e2e/AddressSanitizer/use-after-free/quarantine-free.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t // RUN: %force_device_asan_rt UR_LAYER_ASAN_OPTIONS=quarantine_size_mb:5 UR_LOG_SANITIZER=level:info %{run} %t 2>&1 | FileCheck %s diff --git a/sycl/test-e2e/AddressSanitizer/use-after-free/quarantine-no-free.cpp b/sycl/test-e2e/AddressSanitizer/use-after-free/quarantine-no-free.cpp index 8190ace581b11..0b259a302a552 100644 --- a/sycl/test-e2e/AddressSanitizer/use-after-free/quarantine-no-free.cpp +++ b/sycl/test-e2e/AddressSanitizer/use-after-free/quarantine-no-free.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t // RUN: env UR_LAYER_ASAN_OPTIONS="quarantine_size_mb:5;detect_kernel_arguments:0" UR_LOG_SANITIZER=level:info %{run} not %t 2>&1 | FileCheck %s #include diff --git a/sycl/test-e2e/AddressSanitizer/use-after-free/use-after-free.cpp b/sycl/test-e2e/AddressSanitizer/use-after-free/use-after-free.cpp index 7bc962ce297f6..f839502e20475 100644 --- a/sycl/test-e2e/AddressSanitizer/use-after-free/use-after-free.cpp +++ b/sycl/test-e2e/AddressSanitizer/use-after-free/use-after-free.cpp @@ -1,4 +1,4 @@ -// REQUIRES: linux +// REQUIRES: linux, cpu || (gpu && level_zero) // RUN: %{build} %device_asan_flags -O0 -g -o %t // RUN: env UR_LAYER_ASAN_OPTIONS="quarantine_size_mb:5;detect_kernel_arguments:0" %{run} not %t 2>&1 | FileCheck %s #include