Files
llvm-project/offload/test/api/omp_device_memory.c
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

36 lines
902 B
C

// RUN: %libomptarget-compile-run-and-check-generic
// https://github.com/llvm/llvm-project/issues/182119
// UNSUPPORTED: intelgpu
#include <omp.h>
#include <stdio.h>
#include <assert.h>
int main() {
const int N = 64;
int *device_ptr =
omp_alloc(N * sizeof(int), llvm_omp_target_device_mem_alloc);
#pragma omp target teams distribute parallel for is_device_ptr(device_ptr)
for (int i = 0; i < N; ++i) {
device_ptr[i] = 1;
}
int sum = 0;
#pragma omp target parallel for reduction(+ : sum) is_device_ptr(device_ptr)
for (int i = 0; i < N; ++i)
sum += device_ptr[i];
// CHECK: PASS
if (sum == N)
printf("PASS\n");
omp_free(device_ptr, llvm_omp_target_device_mem_alloc);
// Make sure this interface works.
void *ptr = omp_alloc(0, llvm_omp_target_device_mem_alloc);
assert(!ptr && "Ptr not (nullptr)");
omp_free(ptr, llvm_omp_target_device_mem_alloc);
}