Files
llvm-project/offload/test/offloading/taskloop_offload_nowait.cpp
Nick Sarnie 78ff5b55fd [offload][lit] Enable/disable tests on Level Zero when using DeviceRTL (#182128)
Since we can now build the DeviceRTL with SPIR-V, redo the
`XFAIL/UNSUPPORTED` specifications for the tests we see passing/failing
on the Level Zero backend with the DeviceRTL being used.

The tests marked `UNSUPPORTED` hang or sporadically fail and those are
tracked in https://github.com/llvm/llvm-project/issues/182119.

This change will allow us to enable CI testing with the DeviceRTL.

Here are the full test results with this change applied, running only
the `spirv64-intel` `check-offload` tests:

```
Total Discovered Tests: 453
  Unsupported      : 206 (45.47%)
  Passed           : 141 (31.13%)
  Expectedly Failed: 106 (23.40%)
```

31% is not a bad start.

---------

Signed-off-by: Nick Sarnie <nick.sarnie@intel.com>
2026-02-18 21:53:19 +00:00

43 lines
1.0 KiB
C++

// RUN: %libomptarget-compilexx-and-run-generic
// REQUIRES: gpu
#include <cmath>
#include <cstdlib>
#include <iostream>
bool almost_equal(float x, float gold, float tol) {
if (std::signbit(x) != std::signbit(gold))
x = std::abs(gold) - std::abs(x);
return std::abs(gold) * (1 - tol) <= std::abs(x) &&
std::abs(x) <= std::abs(gold) * (1 + tol);
}
int main(int argc, char *argv[]) {
constexpr const int N0{2};
constexpr const int N1{182};
constexpr const float expected_value{N0 * N1};
float counter_N0{};
#pragma omp target data map(tofrom : counter_N0)
{
#pragma omp taskloop shared(counter_N0)
for (int i0 = 0; i0 < N0; i0++) {
#pragma omp target teams distribute parallel for map(tofrom : counter_N0) nowait
for (int i1 = 0; i1 < N1; i1++) {
#pragma omp atomic update
counter_N0 = counter_N0 + 1.;
}
}
}
if (!almost_equal(counter_N0, expected_value, 0.1)) {
std::cerr << "Expected: " << expected_value << " Got: " << counter_N0
<< '\n';
return -1;
}
return 0;
}