26b777444b
We finally got our buildbot added (to staging, at least) so we want to start running L0 tests in CI. We need `check-offload` to pass though, so XFAIL everything failing. There's a couple `UNSUPPORTED` as well, those are for sporadic fails. Also make set the `gpu` and `intelgpu` LIT variables when testing the `spirv64-intel` triple. We have no DeviceRTL yet so basically everything fails, but we manage to get ``` Total Discovered Tests: 432 Unsupported : 169 (39.12%) Passed : 67 (15.51%) Expectedly Failed: 196 (45.37%) ``` We still don't build the level zero plugin by default and these tests don't run unless the plugin was built, so this has no effect on most builds. --------- Signed-off-by: Nick Sarnie <nick.sarnie@intel.com>
49 lines
1.4 KiB
C
49 lines
1.4 KiB
C
// RUN: %libomptarget-compile-run-and-check-generic
|
|
// XFAIL: intelgpu
|
|
|
|
#include <assert.h>
|
|
#include <stdio.h>
|
|
|
|
#pragma omp begin declare variant match(device = {kind(gpu)})
|
|
// Provided by the runtime.
|
|
void *__llvm_omp_indirect_call_lookup(void *host_ptr);
|
|
#pragma omp declare target to(__llvm_omp_indirect_call_lookup) \
|
|
device_type(nohost)
|
|
#pragma omp end declare variant
|
|
|
|
#pragma omp begin declare variant match(device = {kind(cpu)})
|
|
// We assume unified addressing on the CPU target.
|
|
void *__llvm_omp_indirect_call_lookup(void *host_ptr) { return host_ptr; }
|
|
#pragma omp end declare variant
|
|
|
|
#pragma omp begin declare target indirect
|
|
void foo(int *x) { *x = *x + 1; }
|
|
void bar(int *x) { *x = *x + 1; }
|
|
void baz(int *x) { *x = *x + 1; }
|
|
#pragma omp end declare target
|
|
|
|
int main() {
|
|
void *foo_ptr = foo;
|
|
void *bar_ptr = bar;
|
|
void *baz_ptr = baz;
|
|
|
|
int count = 0;
|
|
void *foo_res;
|
|
void *bar_res;
|
|
void *baz_res;
|
|
#pragma omp target map(to : foo_ptr, bar_ptr, baz_ptr) map(tofrom : count)
|
|
{
|
|
foo_res = __llvm_omp_indirect_call_lookup(foo_ptr);
|
|
((void (*)(int *))foo_res)(&count);
|
|
bar_res = __llvm_omp_indirect_call_lookup(bar_ptr);
|
|
((void (*)(int *))bar_res)(&count);
|
|
baz_res = __llvm_omp_indirect_call_lookup(baz_ptr);
|
|
((void (*)(int *))baz_res)(&count);
|
|
}
|
|
|
|
assert(count == 3 && "Calling failed");
|
|
|
|
// CHECK: PASS
|
|
printf("PASS\n");
|
|
}
|