intel · lbushi25 · May 16, 2024 · May 24, 2024 · Jun 20, 2024 · Jun 20, 2024
@@ -3,7 +3,6 @@
 
 // REQUIRES: opencl-aot, accelerator
 
-// XFAIL: *
 
 // Remove any archives
 // RUN: rm -f %t_*.a

@@ -4,7 +4,6 @@
 // UNSUPPORTED: hip
 //
 // FIXME: Remove XFAIL one intel/llvm#11364 is resolved
-// XFAIL: (opencl && gpu)
 
 // RUN: %{build} -DSYCL_FALLBACK_ASSERT=1 -o %t.out
 // Shouldn't fail on ACC as fallback assert isn't enqueued there

@@ -7,7 +7,6 @@
 // UNSUPPORTED: cuda
 //
 // FIXME: Remove XFAIL one intel/llvm#11364 is resolved
-// XFAIL: (opencl && gpu)
 
 // RUN: %{build} -DSYCL_FALLBACK_ASSERT=1 -I %S/Inputs %S/Inputs/kernels_in_file2.cpp -o %t.out
 // RUN: %{run} %t.out &> %t.txt ; FileCheck %s --input-file %t.txt %if fpga %{ --check-prefix=CHECK-ACC %}

@@ -7,7 +7,6 @@
 // UNSUPPORTED: cuda
 //
 // FIXME: Remove XFAIL one intel/llvm#11364 is resolved
-// XFAIL: (opencl && gpu)
 
 // RUN: %clangxx -DSYCL_FALLBACK_ASSERT=1 -fsycl -fsycl-targets=%{sycl_triple} -DDEFINE_NDEBUG_INFILE2 -I %S/Inputs %S/assert_in_multiple_tus.cpp %S/Inputs/kernels_in_file2.cpp -o %t.out
 // Shouldn't fail on ACC as fallback assert isn't enqueued there

@@ -4,7 +4,6 @@
 // UNSUPPORTED: hip
 //
 // FIXME: Remove XFAIL one intel/llvm#11364 is resolved
-// XFAIL: (opencl && gpu)
 
 // RUN: %{build} -DSYCL_FALLBACK_ASSERT=1 -o %t.out
 // Shouldn't fail on ACC as fallback assert isn't enqueued there

@@ -4,7 +4,6 @@
 // RUN: %{build} -DSYCL_FALLBACK_ASSERT=1 -o %t.out %threads_lib
 //
 // FIXME: Remove XFAIL one intel/llvm#11364 is resolved
-// XFAIL: (opencl && gpu)
 //
 // Since this is a multi-threaded application enable memory tracking and
 // deferred release feature in the Level Zero plugin to avoid releasing memory

@@ -2,7 +2,6 @@
 // UNSUPPORTED: cuda || hip
 //
 // FIXME: Remove XFAIL one intel/llvm#11364 is resolved
-// XFAIL: (opencl && gpu)
 //
 // https://github.com/intel/llvm/issues/12797
 // UNSUPPORTED: windows

@@ -3,7 +3,6 @@
 // UNSUPPORTED: cuda, hip
 //
 // FIXME: Remove XFAIL one intel/llvm#11364 is resolved
-// XFAIL: (opencl && gpu)
 //
 // https://github.com/intel/llvm/issues/12797
 // UNSUPPORTED: windows

@@ -2,7 +2,7 @@
 // RUN: %{run-unfiltered-devices} %t.out
 //
 // Hip is missing some of the parameters tested here so it fails with NVIDIA
-// XFAIL: hip_nvidia
+
 
 //==--------------- aspects.cpp - SYCL device test ------------------------==//
 //

@@ -1,7 +1,6 @@
 // RUN: %{build} -o %t.out
 // RUN: %{run} %t.out
 //
-// XFAIL: level_zero&&gpu
 
 //==---------- reinterpret.cpp --- SYCL buffer reinterpret basic test ------==//
 //

@@ -5,7 +5,6 @@
 // RUN: %{run} %t_var.out | FileCheck %s
 
 // Hits an assertion with AMD:
-// XFAIL: hip_amd
 
 #include <sycl/detail/core.hpp>
 #include <sycl/ext/oneapi/experimental/builtins.hpp>

@@ -30,20 +30,20 @@ void test(bool CheckDevice, double delta, FuncTy F, ExpectedTy Expected,
 
   if (!CheckDevice)
     return;
+
+    sycl::buffer<bool, 1> SuccessBuf{1};
 
-  sycl::buffer<bool, 1> SuccessBuf{1};
-
-  // Make sure we don't use fp64 on devices that don't support it.
-  sycl::detail::get_elem_type_t<ExpectedTy> d(delta);
-
-  sycl::queue{}.submit([&](sycl::handler &cgh) {
-    sycl::accessor Success{SuccessBuf, cgh};
-    cgh.single_task([=]() {
-      auto R = F(Args...);
-      static_assert(std::is_same_v<decltype(Expected), decltype(R)>);
-      Success[0] = equal(R, Expected, d);
+    // Make sure we don't use fp64 on devices that don't support it.
+    sycl::detail::get_elem_type_t<ExpectedTy> d(delta);
+
+    sycl::queue{}.submit([&](sycl::handler &cgh) {
+      sycl::accessor Success{SuccessBuf, cgh};
+      cgh.single_task([=]() {
+        auto R = F(Args...);
+        static_assert(std::is_same_v<decltype(Expected), decltype(R)>);
+        Success[0] = equal(R, Expected, d);
+      });
     });
-  });
   assert(sycl::host_accessor{SuccessBuf}[0]);
 }
 

@@ -1,7 +1,6 @@
 // RUN: %{build} -o %t.out
 // RUN: %{run} %t.out
 // TODO: Remove XFAIL after fixing https://github.com/intel/llvm/issues/13397
-// XFAIL: cpu
 
 #include "helpers.hpp"
 

@@ -3,7 +3,6 @@
 //
 // Returns error "Barrier is not supported on the host device
 // yet." with Nvidia.
-// XFAIL: hip_nvidia
 
 //==--------device_event.cpp - SYCL class device_event test ----------------==//
 //

@@ -3,7 +3,6 @@
 //
 // Appears to fail on HIP Nvidia because 'no device of requested type available'
 // when constructing a queue with an exception_list.
-// XFAIL: hip_nvidia
 //==------------------- handler.cpp ----------------------------------------==//
 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.
 // See https://llvm.org/LICENSE.txt for license information.

@@ -10,7 +10,6 @@
 // RUN: %{run} %t.out
 
 // https://github.com/intel/llvm/issues/13887
-// XFAIL: *
 // If users need to use host pipe feature provided by experimental::pipe, all
 // pipes in their design should use the experimental::pipe (as a workround).
 

@@ -5,7 +5,6 @@
 // UNSUPPORTED: level_zero
 //
 // Consistently fails with opencl gpu, enable when fixed.
-// XFAIL: opencl && gpu
 
 //==--- kernel_info.cpp - SYCL kernel info test ----------------------------==//
 //

@@ -2,7 +2,6 @@
 // RUN: %{run} %t.out
 //
 // Nvidia should not allow sub_devices but does not throw corresponding error.
-// XFAIL: hip_nvidia
 /* Check that:
 1) if partition_equally is supported, then we check that the correct
 invalid errc is returned if more than max_compute_units are requested

@@ -1,7 +1,6 @@
 // RUN: %{build} -o %t.out
 // RUN: %{run} %t.out
 //
-// XFAIL: hip_nvidia
 //==--------------- queue.cpp - SYCL queue test ----------------------------==//
 //
 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.

@@ -1,7 +1,6 @@
 // RUN: %{build} -o %t.out
 // RUN: env SYCL_PI_TRACE=2 %{run} %t.out | FileCheck %s
 //
-// XFAIL: hip_nvidia
 
 #include <sycl/detail/core.hpp>
 int main() {

@@ -2,7 +2,6 @@
 // RUN: %{run} %t.out
 //
 // Fails to release USM pointer on HIP for NVIDIA
-// XFAIL: hip_nvidia
 // REQUIRES: aspect-usm_shared_allocations
 #include <numeric>
 

@@ -1,7 +1,6 @@
 // RUN: %{build} -o %t.out
 // RUN: %{run} %t.out %if !gpu || linux %{ | FileCheck %s %}
 //
-// XFAIL: hip_nvidia
 //==-------------- copy.cpp - SYCL stream obect auto flushing test ---------==//
 //
 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.

@@ -2,7 +2,6 @@
 // RUN: %{run} %t.out
 //
 // Failing negative test with HIP. Temporarily disabled for CUDA.
-// XFAIL: hip, cuda
 
 #include <sycl/detail/core.hpp>
 

@@ -3,7 +3,6 @@
 //
 // hip_nvidia has problems constructing queues due to `No device of requested
 // type available`.
-// XFAIL: hip_nvidia
 //==-------- queue_old_interop.cpp - SYCL queue OpenCL interop test --------==//
 //
 // Part of the LLVM Project, under the Apache License v2.0 with LLVM Exceptions.

@@ -2,7 +2,6 @@
 // RUN: -fsycl-dead-args-optimization
 // RUN: %{run} %t.out
 //
-// XFAIL: hip_nvidia
 
 #include <sycl/detail/core.hpp>
 

@@ -2,7 +2,6 @@
 // RUN: -fsycl-dead-args-optimization
 // RUN: %{run} %t.out
 //
-// XFAIL: hip_nvidia
 
 #include "Inputs/split-per-source.h"
 

@@ -2,7 +2,6 @@
 //
 // FIXME: OpenCL CPU backend compiler crashes on a call to _wassert.
 // Disable the test until the fix reaches SYCL test infrastructure.
-// XFAIL: *
 //
 // RUN: %{build} -o %t.out
 //

@@ -7,7 +7,6 @@
 //===----------------------------------------------------------------------===//
 // RUN: %{build} -fsycl-device-code-split=per_kernel -o %t.out
 // RUN: %{run} %t.out
-// XFAIL: *
 // TODO Remove XFAIL once the simd vector provides move constructor
 //
 // Test for esimd move constructor

@@ -7,7 +7,6 @@
 //===----------------------------------------------------------------------===//
 // RUN: %{build} -fsycl-device-code-split=per_kernel -o %t.out
 // RUN: %{run} %t.out
-// XFAIL: *
 // TODO Remove XFAIL once the simd vector provides move constructor
 //
 // Test for esimd move constructor

@@ -8,7 +8,6 @@
 //===----------------------------------------------------------------------===//
 // RUN: %{build} -fsycl-device-code-split=per_kernel -o %t.out
 // RUN: %{run} %t.out
-// XFAIL: *
 // TODO Remove XFAIL once the simd vector provides move assignment operator
 //
 // Test for simd move and copy assignment operators.

@@ -7,7 +7,6 @@
 // The test still fails after GPU driver update on Linux. Temporary marking it
 // as expected to fail, whilst it is being investigated, see intel/llvm#11359
 // FIXME: remove that XFAIL
-// XFAIL: linux
 
 #include "esimd_test_utils.hpp"
 

@@ -9,8 +9,7 @@
 // RUN: %clangxx -fsycl -fsycl-targets=intel_gpu_bdw %s -Xs "-options -vc-codegen" -o %t.out
 // RUN: %t.out
 // TODO: remove XFAIL when the fix in GPU RT for Windows is updated on CI
-// machines
-// XFAIL: windows
+// machines. See https://github.com/intel/llvm/issues/14336
 // This is basic test to test hardware dispatch functionality with ESIMD.
 
 #include <iostream>

@@ -1,3 +1,2 @@
 REQUIRES: accelerator
 RUN: env SYCL_PI_TRACE=1 %{run} %T/rsbench -s large -l 34 -p 300000 -P 1000 -W 100 -m event
-XFAIL: *
@@ -1,3 +1,2 @@
 REQUIRES: cpu
 RUN: env SYCL_PI_TRACE=1 %{run} %T/rsbench -s large -l 34 -p 300000 -P 1000 -W 100 -m event
-XFAIL: *
@@ -1,3 +1,2 @@
 REQUIRES: gpu
 RUN: env SYCL_PI_TRACE=1 %{run} %T/rsbench -s large -l 34 -p 300000 -P 1000 -W 100 -m event
-XFAIL: *
@@ -11,7 +11,6 @@
 // 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
-// XFAIL: cuda, hip
 // UNSUPPORTED: opencl
 // Note: failing negative test with HIP in the original test
 

@@ -11,7 +11,6 @@
 // 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
-// XFAIL: cuda, hip
 // UNSUPPORTED: opencl
 // Note: failing negative test with HIP in the original test
 

@@ -1,5 +1,3 @@
-// Fails with opencl non-cpu, enable when fixed.
-// XFAIL: (opencl && !cpu && !accelerator)
 // RUN: %{build} -I . -o %t.out
 // RUN: %{run} %t.out
 

@@ -1,7 +1,6 @@
 // RUN: %{build} -o %t.out
 // RUN: %{run} %t.out
 //
-// XFAIL: hip_nvidia
 
 #include <sycl/detail/core.hpp>
 

@@ -1,7 +1,6 @@
 // RUN: %{build} -fno-sycl-early-optimizations -o %t.out
 // RUN: %{run} %t.out
 //
-// XFAIL: hip_nvidia
 
 // The test checks that multiple calls to the same template instantiation of a
 // group local memory function result in separate allocations, even with device

@@ -6,7 +6,6 @@
 // RUN: %{run} %t.out
 // The test is failing when writing directly to output buffer.
 // If temporary variable is used (see TO_PASS mode) the test succeeded.
-// XFAIL: gpu
 #include "include/asmhelper.h"
 #include <iostream>
 #include <vector>

@@ -1,6 +1,5 @@
 // TODO: Passing/returning structures via invoke_simd() API is not implemented
 // in GPU driver yet. Enable the test when GPU RT supports it.
-// XFAIL: gpu
 //
 // RUN: %{build} -DIMPL_SUBGROUP -fno-sycl-device-code-split-esimd -Xclang -fsycl-allow-func-ptr -o %t.out
 // RUN: env IGC_VCSaveStackCallLinkage=1 IGC_VCDirectCallsOnly=1 %{run} %t.out

@@ -1,6 +1,5 @@
 // TODO: Passing/returning structures via invoke_simd() API is not implemented
 // in GPU driver yet. Enable the test when GPU RT supports it.
-// XFAIL: gpu
 //
 // RUN: %{build} -fno-sycl-device-code-split-esimd -Xclang -fsycl-allow-func-ptr -o %t.out
 // RUN: env IGC_VCSaveStackCallLinkage=1 IGC_VCDirectCallsOnly=1 %{run} %t.out

@@ -1,5 +1,4 @@
 // TODO: enable when Jira ticket resolved
-// XFAIL: gpu
 //
 // Check that full compilation works:
 // RUN: %clangxx -DIMPL_SUBGROUP -fsycl -fno-sycl-device-code-split-esimd -Xclang -fsycl-allow-func-ptr %S/../tuple.cpp -o %t.out

@@ -1,5 +1,4 @@
 // TODO: enable when Jira ticket resolved
-// XFAIL: gpu
 //
 // Check that full compilation works:
 // RUN: %clangxx -DIMPL_SUBGROUP -fsycl -fno-sycl-device-code-split-esimd -Xclang -fsycl-allow-func-ptr %S/../tuple_return.cpp -o %t.out

@@ -1,5 +1,4 @@
 // TODO: enable when Jira ticket resolved
-// XFAIL: gpu
 //
 // Check that full compilation works:
 // RUN: %clangxx -DIMPL_SUBGROUP -fsycl -fno-sycl-device-code-split-esimd -Xclang -fsycl-allow-func-ptr %S/../tuple_vadd.cpp -o %t.out

@@ -4,7 +4,6 @@
 // (http://eel.is/c++draft/basic.types.general#def:type,scalar)
 // TODO FIXME: Compile must fail with meaningful error message, but currently it
 // compiles with no error
-// XFAIL: gpu
 /*
  * Test case specification: Test and report errors if accessor argument is
  * passed to invoked ESIMD function

@@ -2,7 +2,6 @@
 //
 // TODO FIXME: Currently compile fail with "no or multiple invoke_simd targets
 // found"
-// XFAIL: gpu
 /*
  * Test case specification: Test and report errors if reference argument is
  * passed to invoked ESIMD function

@@ -2,7 +2,6 @@
 // UNSUPPORTED: gpu-intel-pvc
 //
 // TODO: enable when Jira ticket resolved
-// XFAIL: gpu
 //
 // Check that full compilation works:
 // RUN: %{build} -fno-sycl-device-code-split-esimd -Xclang -fsycl-allow-func-ptr -o %t.out