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
57 lines
1.3 KiB
C++
57 lines
1.3 KiB
C++
// RUN: %libomptarget-compilexx-run-and-check-generic
|
|
|
|
#include <omp.h>
|
|
#include <stdio.h>
|
|
|
|
#define N 1024
|
|
|
|
int A[N];
|
|
int B[N];
|
|
int C[N];
|
|
int main() {
|
|
for (int i = 0; i < N; i++)
|
|
A[i] = B[i] = i;
|
|
|
|
#pragma omp parallel num_threads(2)
|
|
{
|
|
if (omp_get_thread_num() == 1) {
|
|
// map data A & B and move to
|
|
#pragma omp target enter data map(to : A, B) depend(out : A[0]) nowait
|
|
|
|
// no data move since already mapped
|
|
#pragma omp target map(A, B) depend(out : A[0]) nowait
|
|
{
|
|
for (int i = 0; i < N; i++)
|
|
++A[i];
|
|
for (int i = 0; i < N; i++)
|
|
++B[i];
|
|
}
|
|
|
|
// no data move since already mapped
|
|
#pragma omp target teams num_teams(1) map(A, B) depend(out : A[0]) nowait
|
|
{
|
|
for (int i = 0; i < N; i++)
|
|
++A[i];
|
|
for (int i = 0; i < N; i++)
|
|
++B[i];
|
|
}
|
|
|
|
// A updated via update
|
|
#pragma omp target update from(A) depend(out : A[0]) nowait
|
|
|
|
// B updated via exit, A just released
|
|
#pragma omp target exit data map(release : A) map(from : B) depend(out : A[0]) \
|
|
nowait
|
|
} // if
|
|
} // parallel
|
|
|
|
int Sum = 0;
|
|
for (int i = 0; i < N; i++)
|
|
Sum += A[i] + B[i];
|
|
// Sum is 2 * N * (2 + N - 1 + 2) / 2
|
|
// CHECK: Sum = 1051648.
|
|
printf("Sum = %d.\n", Sum);
|
|
|
|
return Sum != 2 * N * (2 + N - 1 + 2) / 2;
|
|
}
|