diff --git a/sycl/test-e2e/Basic/device_event.cpp b/sycl/test-e2e/Basic/device_event.cpp index c306fa69c4538..a9eabcead3166 100644 --- a/sycl/test-e2e/Basic/device_event.cpp +++ b/sycl/test-e2e/Basic/device_event.cpp @@ -1,6 +1,9 @@ // RUN: %{build} -o %t.run // RUN: %{run} %t.run +// UNSUPPORTED: spirv-backend +// UNSUPPORTED-TRACKER: CMPLRLLVM-64705 + //==--------device_event.cpp - SYCL class device_event test ----------------==// // // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. diff --git a/sycl/test-e2e/Basic/image/image.cpp b/sycl/test-e2e/Basic/image/image.cpp index a14cf9b63be33..f1734918153d1 100644 --- a/sycl/test-e2e/Basic/image/image.cpp +++ b/sycl/test-e2e/Basic/image/image.cpp @@ -2,9 +2,6 @@ // RUN: %{build} -o %t.out // RUN: %{run} %t.out -// XFAIL: spirv-backend && gpu-intel-dg2 -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160589 - //==------------------- image.cpp - SYCL image basic test -----------------==// // // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. diff --git a/sycl/test-e2e/Basic/image/image_array.cpp b/sycl/test-e2e/Basic/image/image_array.cpp index 2327b9f63421f..2bf1f57540906 100644 --- a/sycl/test-e2e/Basic/image/image_array.cpp +++ b/sycl/test-e2e/Basic/image/image_array.cpp @@ -3,9 +3,6 @@ // RUN: %{build} -o %t.out // RUN: %{run} %t.out -// XFAIL: spirv-backend && gpu-intel-dg2 -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160589 - //==------------------- image.cpp - SYCL image basic test -----------------==// // // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions. diff --git a/sycl/test-e2e/Basic/image/lit.local.cfg b/sycl/test-e2e/Basic/image/lit.local.cfg index 6998c0659f302..8ce73f3911718 100644 --- a/sycl/test-e2e/Basic/image/lit.local.cfg +++ b/sycl/test-e2e/Basic/image/lit.local.cfg @@ -5,7 +5,7 @@ # # Legacy images aren't supported on AMD and also don't compile, so mark them # unsupported here. Bindless images should be used instead. -config.unsupported_features += ['target-amd'] +config.unsupported_features += ['spirv-backend', 'target-amd'] # Legacy images aren't supported on Native CPU. Bindless images should be used # instead when they are working. diff --git a/sycl/test-e2e/NonUniformGroups/chunk_algorithms.cpp b/sycl/test-e2e/NonUniformGroups/chunk_algorithms.cpp index 3285ed8691f4f..2bc1c39e47d15 100644 --- a/sycl/test-e2e/NonUniformGroups/chunk_algorithms.cpp +++ b/sycl/test-e2e/NonUniformGroups/chunk_algorithms.cpp @@ -11,6 +11,10 @@ // UNSUPPORTED: target-amd // UNSUPPORTED-INTENDED: fixed_size_group aspect not available on amd +// UNSUPPORTED: spirv-backend +// UNSUPPORTED-TRACKER: CMPLRLLVM-64702 +// The test is disabled for spirv-backend while we investigate the root cause. + // XFAIL: target-native_cpu // XFAIL-TRACKER: https://github.com/intel/llvm/issues/20142 diff --git a/sycl/test-e2e/NonUniformGroups/fragment_algorithms.cpp b/sycl/test-e2e/NonUniformGroups/fragment_algorithms.cpp index 563bb98ce7b1e..4c7093127c02a 100644 --- a/sycl/test-e2e/NonUniformGroups/fragment_algorithms.cpp +++ b/sycl/test-e2e/NonUniformGroups/fragment_algorithms.cpp @@ -13,6 +13,10 @@ // UNSUPPORTED: cuda // UNSUPPORTED-TRACKER: https://github.com/intel/llvm/issues/12995 +// UNSUPPORTED: spirv-backend +// UNSUPPORTED-TRACKER: CMPLRLLVM-64702 +// The test is disabled for spirv-backend while we investigate the root cause. + #include #include #include diff --git a/sycl/test-e2e/Reduction/reduction_span.cpp b/sycl/test-e2e/Reduction/reduction_span.cpp index 04a0f34175dbc..b96107a4c5674 100644 --- a/sycl/test-e2e/Reduction/reduction_span.cpp +++ b/sycl/test-e2e/Reduction/reduction_span.cpp @@ -3,6 +3,10 @@ // This test performs basic checks of reductions initialized with a sycl::span +// Depends on SPIR-V Backend & run-time drivers version. +// XFAIL: spirv-backend && cpu +// XFAIL-TRACKER: CMPLRLLVM-64705 + #include #include diff --git a/sycl/test-e2e/Reduction/reduction_span_pack.cpp b/sycl/test-e2e/Reduction/reduction_span_pack.cpp index daa29f68d01a9..e101dfab842e5 100644 --- a/sycl/test-e2e/Reduction/reduction_span_pack.cpp +++ b/sycl/test-e2e/Reduction/reduction_span_pack.cpp @@ -4,6 +4,10 @@ // This test performs basic checks of reductions initialized with a pack // containing at least one sycl::span +// Depends on SPIR-V Backend & run-time drivers version. +// XFAIL: spirv-backend && cpu +// XFAIL-TRACKER: CMPLRLLVM-64705 + #include #include diff --git a/sycl/test-e2e/Regression/group_load_fortified.cpp b/sycl/test-e2e/Regression/group_load_fortified.cpp index ffa067221752f..c7b1287548a38 100644 --- a/sycl/test-e2e/Regression/group_load_fortified.cpp +++ b/sycl/test-e2e/Regression/group_load_fortified.cpp @@ -2,6 +2,10 @@ // RUN: %{build} -D_FORTIFY_SOURCE=2 -o %t.out // RUN: %{run} %t.out +// Depends on SPIR-V Backend & run-time drivers version. +// XFAIL: spirv-backend && cpu +// XFAIL-TRACKER: CMPLRLLVM-64705 + // Checks that group_load runs even when the source code is fortified. This // failed at one point due to the use of std::memcpy in the implementation, // which would hold an assert in device code when fortified, which would fail diff --git a/sycl/test-e2e/Sampler/lit.local.cfg b/sycl/test-e2e/Sampler/lit.local.cfg index a2540de045655..d5363329efec4 100644 --- a/sycl/test-e2e/Sampler/lit.local.cfg +++ b/sycl/test-e2e/Sampler/lit.local.cfg @@ -8,7 +8,7 @@ # # Legacy images aren't supported on AMD and also don't compile, so mark them # unsupported here. Bindless images should be used instead. -config.unsupported_features += ['target-amd'] +config.unsupported_features += ['spirv-backend', 'target-amd'] # Legacy images aren't supported on Native CPU. Use bindless_images when working. # https://github.com/intel/llvm/issues/20142 diff --git a/sycl/test-e2e/ThreadSanitizer/aot/gpu.cpp b/sycl/test-e2e/ThreadSanitizer/aot/gpu.cpp index 9bc97469f5eda..3c0935cad742b 100644 --- a/sycl/test-e2e/ThreadSanitizer/aot/gpu.cpp +++ b/sycl/test-e2e/ThreadSanitizer/aot/gpu.cpp @@ -13,6 +13,3 @@ // RUN: %{run-aux} %{build} %device_tsan_aot_flags -O3 -g %S/Inputs/usm_data_race.cpp -o %t.out // RUN: %{run} %t.out 2>&1 | FileCheck %S/Inputs/usm_data_race.cpp - -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 diff --git a/sycl/test-e2e/ThreadSanitizer/check_buffer.cpp b/sycl/test-e2e/ThreadSanitizer/check_buffer.cpp index 22f61faffdaaa..177335dbf0048 100644 --- a/sycl/test-e2e/ThreadSanitizer/check_buffer.cpp +++ b/sycl/test-e2e/ThreadSanitizer/check_buffer.cpp @@ -5,9 +5,6 @@ // RUN: %{build} %device_tsan_flags -O2 -g -o %t2.out // RUN: %{run} %t2.out 2>&1 | FileCheck %s -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 - #include static const int N = 128; diff --git a/sycl/test-e2e/ThreadSanitizer/check_device_global.cpp b/sycl/test-e2e/ThreadSanitizer/check_device_global.cpp index b97de1a634a34..67c302c06a01f 100644 --- a/sycl/test-e2e/ThreadSanitizer/check_device_global.cpp +++ b/sycl/test-e2e/ThreadSanitizer/check_device_global.cpp @@ -4,10 +4,6 @@ // RUN: %{run} %t1.out 2>&1 | FileCheck %s // RUN: %{build} %device_tsan_flags -O2 -g -o %t2.out // RUN: %{run} %t2.out 2>&1 | FileCheck %s - -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 - #include #include diff --git a/sycl/test-e2e/ThreadSanitizer/check_device_usm.cpp b/sycl/test-e2e/ThreadSanitizer/check_device_usm.cpp index 4c53ee4505d43..907252f7a01ed 100644 --- a/sycl/test-e2e/ThreadSanitizer/check_device_usm.cpp +++ b/sycl/test-e2e/ThreadSanitizer/check_device_usm.cpp @@ -2,10 +2,6 @@ // ALLOW_RETRIES: 10 // RUN: %{build} %device_tsan_flags -O0 -g -o %t.out // RUN: %{run} %t.out 2>&1 | FileCheck %s - -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 - #include "sycl/detail/core.hpp" #include "sycl/usm.hpp" diff --git a/sycl/test-e2e/ThreadSanitizer/check_host_usm.cpp b/sycl/test-e2e/ThreadSanitizer/check_host_usm.cpp index f4d48847bbbd5..33f12be23121b 100644 --- a/sycl/test-e2e/ThreadSanitizer/check_host_usm.cpp +++ b/sycl/test-e2e/ThreadSanitizer/check_host_usm.cpp @@ -2,10 +2,6 @@ // ALLOW_RETRIES: 10 // RUN: %{build} %device_tsan_flags -O0 -g -o %t.out // RUN: %{run} %t.out 2>&1 | FileCheck %s - -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 - #include "sycl/detail/core.hpp" #include "sycl/usm.hpp" diff --git a/sycl/test-e2e/ThreadSanitizer/check_shared_usm.cpp b/sycl/test-e2e/ThreadSanitizer/check_shared_usm.cpp index 7c977be56d9e6..e471e71538d80 100644 --- a/sycl/test-e2e/ThreadSanitizer/check_shared_usm.cpp +++ b/sycl/test-e2e/ThreadSanitizer/check_shared_usm.cpp @@ -2,10 +2,6 @@ // ALLOW_RETRIES: 10 // RUN: %{build} %device_tsan_flags -O0 -g -o %t.out // RUN: %{run} %t.out 2>&1 | FileCheck %s - -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 - #include "sycl/detail/core.hpp" #include "sycl/usm.hpp" diff --git a/sycl/test-e2e/ThreadSanitizer/check_sub_buffer.cpp b/sycl/test-e2e/ThreadSanitizer/check_sub_buffer.cpp index 1819798b192bc..82e63a1376680 100644 --- a/sycl/test-e2e/ThreadSanitizer/check_sub_buffer.cpp +++ b/sycl/test-e2e/ThreadSanitizer/check_sub_buffer.cpp @@ -5,9 +5,6 @@ // RUN: %{build} %device_tsan_flags -O2 -g -o %t2.out // RUN: %{run} %t2.out 2>&1 | FileCheck %s -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 - #include int main() { diff --git a/sycl/test-e2e/ThreadSanitizer/group_local_memory.cpp b/sycl/test-e2e/ThreadSanitizer/group_local_memory.cpp index 16433ecbfa101..c843ce694c71c 100644 --- a/sycl/test-e2e/ThreadSanitizer/group_local_memory.cpp +++ b/sycl/test-e2e/ThreadSanitizer/group_local_memory.cpp @@ -2,10 +2,6 @@ // ALLOW_RETRIES: 10 // RUN: %{build} %device_tsan_flags -O0 -g -o %t.out // RUN: %{run} %t.out 2>&1 | FileCheck %s - -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 - #include "sycl/ext/oneapi/group_local_memory.hpp" #include "sycl/detail/core.hpp" #include "sycl/usm.hpp" diff --git a/sycl/test-e2e/ThreadSanitizer/lit.local.cfg b/sycl/test-e2e/ThreadSanitizer/lit.local.cfg index 63a387034a132..f87387034bc0c 100644 --- a/sycl/test-e2e/ThreadSanitizer/lit.local.cfg +++ b/sycl/test-e2e/ThreadSanitizer/lit.local.cfg @@ -11,6 +11,9 @@ config.unsupported_features += ['target-nvidia', 'target-amd'] # TRACKER: https://github.com/intel/llvm/issues/16184 config.unsupported_features += ['gpu-intel-gen12', 'gpu-intel-dg2'] +# CMPLRLLVM-64052 +config.unsupported_features += ['spirv-backend'] + # https://github.com/intel/llvm/issues/16920 config.unsupported_features += ['arch-intel_gpu_bmg_g21'] diff --git a/sycl/test-e2e/ThreadSanitizer/local_accessor.cpp b/sycl/test-e2e/ThreadSanitizer/local_accessor.cpp index fa3e152d4dd6a..9a8292c1160fa 100644 --- a/sycl/test-e2e/ThreadSanitizer/local_accessor.cpp +++ b/sycl/test-e2e/ThreadSanitizer/local_accessor.cpp @@ -2,10 +2,6 @@ // ALLOW_RETRIES: 10 // RUN: %{build} %device_tsan_flags -O0 -g -o %t.out // RUN: %{run} %t.out 2>&1 | FileCheck %s - -// XFAIL: spirv-backend && arch-intel_gpu_pvc -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160602 - #include "sycl/detail/core.hpp" #include "sycl/usm.hpp" diff --git a/sycl/test-e2e/USM/copy.cpp b/sycl/test-e2e/USM/copy.cpp index 7d85f3951fa06..c386e31227a89 100644 --- a/sycl/test-e2e/USM/copy.cpp +++ b/sycl/test-e2e/USM/copy.cpp @@ -9,6 +9,9 @@ // RUN: %{build} -fsycl-device-code-split=per_kernel -o %t1.out // RUN: %{run} %t1.out +// UNSUPPORTED: spirv-backend && arch-intel_gpu_bmg_g21 +// UNSUPPORTED-TRACKER: CMPLRLLVM-64705 + #include #include diff --git a/sycl/test-e2e/USM/memops2d/copy2d_device_to_host.cpp b/sycl/test-e2e/USM/memops2d/copy2d_device_to_host.cpp index 5936a002aef9e..d26bdbb7dd399 100644 --- a/sycl/test-e2e/USM/memops2d/copy2d_device_to_host.cpp +++ b/sycl/test-e2e/USM/memops2d/copy2d_device_to_host.cpp @@ -13,9 +13,6 @@ // UNSUPPORTED: hip // UNSUPPORTED-TRACKER: https://github.com/intel/llvm/issues/10157 -// XFAIL: spirv-backend && gpu-intel-dg2 -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160892 - #include "copy2d_common.hpp" int main() { return test(); } diff --git a/sycl/test-e2e/USM/memops2d/lit.local.cfg b/sycl/test-e2e/USM/memops2d/lit.local.cfg new file mode 100644 index 0000000000000..95f9ce6d4eec3 --- /dev/null +++ b/sycl/test-e2e/USM/memops2d/lit.local.cfg @@ -0,0 +1,5 @@ +# This feature refers to an unsupported capability in the SPIR-V Backend, +# pending triaging and identifying required features/extensions. +# Temporarily disabled until the failure is addressed: +# https://github.com/llvm/llvm-project/issues/127791 +config.unsupported_features += ['spirv-backend'] diff --git a/sycl/test-e2e/USM/memops2d/memcpy2d_device_to_host.cpp b/sycl/test-e2e/USM/memops2d/memcpy2d_device_to_host.cpp index 7fb31a2b01d93..934c75ff9e778 100644 --- a/sycl/test-e2e/USM/memops2d/memcpy2d_device_to_host.cpp +++ b/sycl/test-e2e/USM/memops2d/memcpy2d_device_to_host.cpp @@ -13,9 +13,6 @@ // UNSUPPORTED: hip // UNSUPPORTED-TRACKER: https://github.com/intel/llvm/issues/10157 -// XFAIL: spirv-backend && gpu-intel-dg2 -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160892 - #include "memcpy2d_common.hpp" int main() { return test(); } diff --git a/sycl/test-e2e/bindless_images/array/read_write_unsampled_array.cpp b/sycl/test-e2e/bindless_images/array/read_write_unsampled_array.cpp index 0b84d56a24be8..51080c3f7d57f 100644 --- a/sycl/test-e2e/bindless_images/array/read_write_unsampled_array.cpp +++ b/sycl/test-e2e/bindless_images/array/read_write_unsampled_array.cpp @@ -4,9 +4,6 @@ // RUN: %{build} -o %t.out // RUN: %{run} env NEOReadDebugKeys=1 UseBindlessMode=1 UseExternalAllocatorForSshAndDsh=1 %t.out -// XFAIL: spirv-backend && gpu-intel-dg2 -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160893 - #include "../helpers/common.hpp" #include #include diff --git a/sycl/test-e2e/bindless_images/lit.local.cfg b/sycl/test-e2e/bindless_images/lit.local.cfg index 6b2103442fb66..a03e60ba97420 100644 --- a/sycl/test-e2e/bindless_images/lit.local.cfg +++ b/sycl/test-e2e/bindless_images/lit.local.cfg @@ -1,3 +1,7 @@ +# Support of this feature is waiting for the upstream PR +# https://github.com/llvm/llvm-project/pull/127737 to be merged with intel/llvm. +config.unsupported_features += ['spirv-backend'] + # https://github.com/intel/llvm/issues/20142 config.unsupported_features += ['target-native_cpu'] diff --git a/sycl/test-e2e/bindless_images/read_write_unsampled.cpp b/sycl/test-e2e/bindless_images/read_write_unsampled.cpp index 3351e29fe8b37..8e05df4333cea 100644 --- a/sycl/test-e2e/bindless_images/read_write_unsampled.cpp +++ b/sycl/test-e2e/bindless_images/read_write_unsampled.cpp @@ -6,9 +6,6 @@ // RUN: %{build} -o %t.out // RUN: %{run-unfiltered-devices} env NEOReadDebugKeys=1 UseBindlessMode=1 UseExternalAllocatorForSshAndDsh=1 %t.out -// XFAIL: spirv-backend && gpu-intel-dg2 -// XFAIL-TRACKER: https://github.com/llvm/llvm-project/issues/160893 - #include "helpers/common.hpp" #include #include