5e7e097888
- Remove UNSUPPORTED: intelgpu from 12 passing tests: * mapping/data_member_ref.cpp * offloading/bug50022.cpp, info.c * offloading/target_critical_region.cpp, target_depend_nowait.cpp, target_nowait_target.cpp * offloading/strided_update/* (6 tests) * unified_shared_memory/close_member.c - Change CUDA tests from XFAIL to UNSUPPORTED for Intel GPU: * offloading/CUDA/basic_launch.cu * offloading/CUDA/basic_launch_blocks_and_threads.cu * offloading/CUDA/basic_launch_multi_arg.cu * offloading/CUDA/launch_tu.cu - Add Intel GPU configuration section to lit.cfg to disable USM tests by default
42 lines
1.2 KiB
Plaintext
42 lines
1.2 KiB
Plaintext
// clang-format off
|
|
// RUN: %clang++ %flags -foffload-via-llvm --offload-arch=native %s -o %t
|
|
// RUN: %t | %fcheck-generic
|
|
// RUN: %clang++ %flags -foffload-via-llvm --offload-arch=native %s -o %t -fopenmp
|
|
// RUN: %t | %fcheck-generic
|
|
// clang-format on
|
|
|
|
// REQUIRES: gpu
|
|
// UNSUPPORTED: intelgpu
|
|
|
|
#include <stdio.h>
|
|
|
|
extern "C" {
|
|
void *llvm_omp_target_alloc_shared(size_t Size, int DeviceNum);
|
|
void llvm_omp_target_free_shared(void *DevicePtr, int DeviceNum);
|
|
}
|
|
|
|
__global__ void square(int *Dst, short Q, int *Src, short P) {
|
|
*Dst = (Src[0] + Src[1]) * (Q + P);
|
|
Src[0] = Q;
|
|
Src[1] = P;
|
|
}
|
|
|
|
int main(int argc, char **argv) {
|
|
int DevNo = 0;
|
|
int *Ptr = reinterpret_cast<int *>(llvm_omp_target_alloc_shared(4, DevNo));
|
|
int *Src = reinterpret_cast<int *>(llvm_omp_target_alloc_shared(8, DevNo));
|
|
*Ptr = 7;
|
|
Src[0] = -2;
|
|
Src[1] = 8;
|
|
printf("Ptr %p, *Ptr: %i\n", Ptr, *Ptr);
|
|
// CHECK: Ptr [[Ptr:0x.*]], *Ptr: 7
|
|
printf("Src: %i : %i\n", Src[0], Src[1]);
|
|
// CHECK: Src: -2 : 8
|
|
square<<<1, 1>>>(Ptr, 3, Src, 4);
|
|
printf("Ptr %p, *Ptr: %i\n", Ptr, *Ptr);
|
|
// CHECK: Ptr [[Ptr]], *Ptr: 42
|
|
printf("Src: %i : %i\n", Src[0], Src[1]);
|
|
// CHECK: Src: 3 : 4
|
|
llvm_omp_target_free_shared(Ptr, DevNo);
|
|
}
|