364 lines · cpp
1// RUN: %clang_cc1 -verify -fopenmp -fopenmp-version=45 -ast-print %s -Wno-openmp-mapping | FileCheck %s --check-prefix=CHECK --check-prefix=OMP452// RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping3// RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -std=c++11 -include-pch %t -verify %s -ast-print -Wno-openmp-mapping | FileCheck %s --check-prefix=CHECK --check-prefix=OMP454// RUN: %clang_cc1 -verify -fopenmp -fopenmp-version=50 -ast-print %s -Wno-openmp-mapping -DOMP5 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP505// RUN: %clang_cc1 -fopenmp -fopenmp-version=50 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping -DOMP56// RUN: %clang_cc1 -fopenmp -fopenmp-version=50 -std=c++11 -include-pch %t -verify %s -ast-print -Wno-openmp-mapping -DOMP5 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP507// RUN: %clang_cc1 -verify -fopenmp -ast-print %s -Wno-openmp-mapping -DOMP51 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP518// RUN: %clang_cc1 -fopenmp -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping -DOMP519// RUN: %clang_cc1 -fopenmp -std=c++11 -include-pch %t -verify %s -ast-print -Wno-openmp-mapping -DOMP51 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5110// RUN: %clang_cc1 -verify -fopenmp -fopenmp-version=52 -ast-print %s -Wno-openmp-mapping -DOMP52 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5211// RUN: %clang_cc1 -fopenmp -fopenmp-version=52 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping -DOMP5212// RUN: %clang_cc1 -fopenmp -fopenmp-version=52 -std=c++11 -include-pch %t -verify %s -ast-print -Wno-openmp-mapping -DOMP52 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5213 14// RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-version=45 -ast-print %s -Wno-openmp-mapping | FileCheck %s --check-prefix=CHECK --check-prefix=OMP4515// RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=45 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping16// RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=45 -std=c++11 -include-pch %t -verify %s -ast-print -Wno-openmp-mapping | FileCheck %s --check-prefix=CHECK --check-prefix=OMP4517// RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-version=50 -ast-print %s -Wno-openmp-mapping -DOMP5 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5018// RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=50 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping -DOMP519// RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=50 -std=c++11 -include-pch %t -verify %s -ast-print -Wno-openmp-mapping -DOMP5 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5020// RUN: %clang_cc1 -verify -fopenmp-simd -ast-print %s -Wno-openmp-mapping -DOMP51 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5121// RUN: %clang_cc1 -fopenmp-simd -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping -DOMP5122// RUN: %clang_cc1 -fopenmp-simd -std=c++11 -include-pch %t -verify %s -ast-print -Wno-openmp-mapping -DOMP51 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5123// expected-no-diagnostics24// RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-version=52 -ast-print %s -Wno-openmp-mapping -DOMP52 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5225// RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=52 -x c++ -std=c++11 -emit-pch -o %t %s -Wno-openmp-mapping -DOMP5226// RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=52 -std=c++11 -include-pch %t -verify %s -ast-print -Wno-openmp-mapping -DOMP52 | FileCheck %s --check-prefix=CHECK --check-prefix=OMP5227// expected-no-diagnostics28 29#ifndef HEADER30#define HEADER31 32typedef void **omp_allocator_handle_t;33extern const omp_allocator_handle_t omp_null_allocator;34extern const omp_allocator_handle_t omp_default_mem_alloc;35extern const omp_allocator_handle_t omp_large_cap_mem_alloc;36extern const omp_allocator_handle_t omp_const_mem_alloc;37extern const omp_allocator_handle_t omp_high_bw_mem_alloc;38extern const omp_allocator_handle_t omp_low_lat_mem_alloc;39extern const omp_allocator_handle_t omp_cgroup_mem_alloc;40extern const omp_allocator_handle_t omp_pteam_mem_alloc;41extern const omp_allocator_handle_t omp_thread_mem_alloc;42 43void foo() {}44 45struct S {46 S(): a(0) {}47 S(int v) : a(v) {}48 int a;49 typedef int type;50};51 52template <typename T>53class S7 : public T {54protected:55 T a;56 S7() : a(0) {}57 58public:59 S7(typename T::type v) : a(v) {60#pragma omp target parallel for simd private(a) private(this->a) private(T::a)61 for (int k = 0; k < a.a; ++k)62 ++this->a.a;63 }64 S7 &operator=(S7 &s) {65#pragma omp target parallel for simd private(a) private(this->a)66 for (int k = 0; k < s.a.a; ++k)67 ++s.a.a;68 return *this;69 }70};71 72// CHECK: #pragma omp target parallel for simd private(this->a) private(this->a) private(T::a){{$}}73// CHECK: #pragma omp target parallel for simd private(this->a) private(this->a)74// CHECK: #pragma omp target parallel for simd private(this->a) private(this->a) private(this->S::a)75 76class S8 : public S7<S> {77 S8() {}78 79public:80 S8(int v) : S7<S>(v){81#pragma omp target parallel for simd private(a) private(this->a) private(S7<S>::a)82 for (int k = 0; k < a.a; ++k)83 ++this->a.a;84 }85 S8 &operator=(S8 &s) {86#pragma omp target parallel for simd private(a) private(this->a)87 for (int k = 0; k < s.a.a; ++k)88 ++s.a.a;89 return *this;90 }91};92 93// CHECK: #pragma omp target parallel for simd private(this->a) private(this->a) private(this->S7<S>::a)94// CHECK: #pragma omp target parallel for simd private(this->a) private(this->a)95 96template <class T, int N>97T tmain(T argc, T *argv) {98 T b = argc, c, d, e, f, h;99 T arr[N][10], arr1[N];100 T i, j;101 T s;102 static T a;103// CHECK: static T a;104 static T g;105 const T clen = 5;106// CHECK: T clen = 5;107#pragma omp threadprivate(g)108#pragma omp target parallel for simd schedule(dynamic) default(none) linear(a) allocate(a)109 // CHECK: #pragma omp target parallel for simd schedule(dynamic) default(none) linear(a) allocate(a)110 for (T i = 0; i < 2; ++i)111 a = 2;112// CHECK-NEXT: for (T i = 0; i < 2; ++i)113// CHECK-NEXT: a = 2;114#pragma omp target parallel for simd allocate(d) private(argc, b), firstprivate(c, d), lastprivate(d, f) collapse(N) schedule(static, N) ordered if (parallel :argc) num_threads(N) default(shared) shared(e) reduction(+ : h)115 for (int i = 0; i < 2; ++i)116 for (int j = 0; j < 2; ++j)117 for (int j = 0; j < 2; ++j)118 for (int j = 0; j < 2; ++j)119 for (int j = 0; j < 2; ++j)120 foo();121 // CHECK-NEXT: #pragma omp target parallel for simd allocate(d) private(argc,b) firstprivate(c,d) lastprivate(d,f) collapse(N) schedule(static, N) ordered if(parallel: argc) num_threads(N) default(shared) shared(e) reduction(+: h)122 // CHECK-NEXT: for (int i = 0; i < 2; ++i)123 // CHECK-NEXT: for (int j = 0; j < 2; ++j)124 // CHECK-NEXT: for (int j = 0; j < 2; ++j)125 // CHECK-NEXT: for (int j = 0; j < 2; ++j)126 // CHECK-NEXT: for (int j = 0; j < 2; ++j)127 // CHECK-NEXT: foo();128 129#pragma omp target parallel for simd default(none), private(argc,b) firstprivate(argv) shared (d) if(parallel:argc > 0) num_threads(N) proc_bind(master) reduction(+:c, arr1[argc]) reduction(max:e, arr[:N][0:10])130 for (T i = 0; i < 2; ++i) {}131 // CHECK: #pragma omp target parallel for simd default(none) private(argc,b) firstprivate(argv) shared(d) if(parallel: argc > 0) num_threads(N) proc_bind(master) reduction(+: c,arr1[argc]) reduction(max: e,arr[:N][0:10])132 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {133 // CHECK-NEXT: }134 135#pragma omp target parallel for simd if(N) num_threads(s) proc_bind(close) reduction(^:e, f, arr[0:N][:argc]) reduction(&& : h)136 for (T i = 0; i < 2; ++i) {}137 // CHECK: #pragma omp target parallel for simd if(N) num_threads(s) proc_bind(close) reduction(^: e,f,arr[0:N][:argc]) reduction(&&: h)138 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {139 // CHECK-NEXT: }140 141#if defined(OMP51) || defined(OMP52)142#pragma omp target parallel for simd if(target:argc > 0) if (simd: argc) nontemporal(argc, c, d) order(unconstrained:concurrent) allocate(omp_high_bw_mem_alloc:f) private(f) uses_allocators(omp_high_bw_mem_alloc)143#elif OMP5144#pragma omp target parallel for simd if(target:argc > 0) if (simd: argc) nontemporal(argc, c, d) order(concurrent) allocate(omp_high_bw_mem_alloc:f) private(f) uses_allocators(omp_high_bw_mem_alloc)145#else146#pragma omp target parallel for simd if(target:argc > 0)147#endif // OMP51148 for (T i = 0; i < 2; ++i) {}149 // OMP45: #pragma omp target parallel for simd if(target: argc > 0)150 // OMP50: #pragma omp target parallel for simd if(target: argc > 0) if(simd: argc) nontemporal(argc,c,d) order(concurrent) allocate(omp_high_bw_mem_alloc: f) private(f) uses_allocators(omp_high_bw_mem_alloc)151 // OMP51: #pragma omp target parallel for simd if(target: argc > 0) if(simd: argc) nontemporal(argc,c,d) order(unconstrained: concurrent) allocate(omp_high_bw_mem_alloc: f) private(f) uses_allocators(omp_high_bw_mem_alloc)152 // OMP52: #pragma omp target parallel for simd if(target: argc > 0) if(simd: argc) nontemporal(argc,c,d) order(unconstrained: concurrent) allocate(omp_high_bw_mem_alloc: f) private(f) uses_allocators(omp_high_bw_mem_alloc)153 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {154 // CHECK-NEXT: }155 156#pragma omp target parallel for simd if(parallel:argc > 0)157 for (T i = 0; i < 2; ++i) {}158 // CHECK: #pragma omp target parallel for simd if(parallel: argc > 0)159 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {160 // CHECK-NEXT: }161 162#pragma omp target parallel for simd if(N)163 for (T i = 0; i < 2; ++i) {}164 // CHECK: #pragma omp target parallel for simd if(N)165 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {166 // CHECK-NEXT: }167 168#pragma omp target parallel for simd map(i)169 for (T i = 0; i < 2; ++i) {}170 // CHECK: #pragma omp target parallel for simd map(tofrom: i)171 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {172 // CHECK-NEXT: }173 174#pragma omp target parallel for simd map(arr1[0:10], i)175 for (T i = 0; i < 2; ++i) {}176 // CHECK: #pragma omp target parallel for simd map(tofrom: arr1[0:10],i)177 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {178 // CHECK-NEXT: }179 180#pragma omp target parallel for simd map(to: i) map(from: j)181 for (T i = 0; i < 2; ++i) {}182 // CHECK: #pragma omp target parallel for simd map(to: i) map(from: j)183 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {184 // CHECK-NEXT: }185 186#pragma omp target parallel for simd map(always,alloc: i)187 for (T i = 0; i < 2; ++i) {}188 // CHECK: #pragma omp target parallel for simd map(always,alloc: i)189 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {190 // CHECK-NEXT: }191 192#pragma omp target parallel for simd nowait193 for (T i = 0; i < 2; ++i) {}194 // CHECK: #pragma omp target parallel for simd nowait195 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {196 // CHECK-NEXT: }197 198#pragma omp target parallel for simd depend(in : argc, arr[i:argc], arr1[:])199 for (T i = 0; i < 2; ++i) {}200 // CHECK: #pragma omp target parallel for simd depend(in : argc,arr[i:argc],arr1[:])201 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {202 // CHECK-NEXT: }203 204#pragma omp target parallel for simd defaultmap(tofrom: scalar)205 for (T i = 0; i < 2; ++i) {}206 // CHECK: #pragma omp target parallel for simd defaultmap(tofrom: scalar)207 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {208 // CHECK-NEXT: }209 210#pragma omp target parallel for simd safelen(clen-1)211 for (T i = 0; i < 2; ++i) {}212 // CHECK: #pragma omp target parallel for simd safelen(clen - 1)213 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {214 // CHECK-NEXT: }215 216#pragma omp target parallel for simd simdlen(clen-1)217 for (T i = 0; i < 2; ++i) {}218 // CHECK: #pragma omp target parallel for simd simdlen(clen - 1)219 // CHECK-NEXT: for (T i = 0; i < 2; ++i) {220 // CHECK-NEXT: }221 222#pragma omp target parallel for simd aligned(arr1:N-1)223 for (T i = 0; i < N; ++i) {}224 // CHECK: #pragma omp target parallel for simd aligned(arr1: N - 1)225 // CHECK-NEXT: for (T i = 0; i < N; ++i) {226 // CHECK-NEXT: }227 228 return T();229}230 231int main(int argc, char **argv) {232 int b = argc, c, d, e, f, h;233 int arr[5][10], arr1[5];234 int i, j;235 int s;236 static int a;237// CHECK: static int a;238 const int clen = 5;239// CHECK: int clen = 5;240 static float g;241#pragma omp threadprivate(g)242#pragma omp target parallel for simd schedule(guided, argc) default(none) linear(a) shared(argc)243 // CHECK: #pragma omp target parallel for simd schedule(guided, argc) default(none) linear(a) shared(argc)244 for (int i = 0; i < 2; ++i)245 a = 2;246// CHECK-NEXT: for (int i = 0; i < 2; ++i)247// CHECK-NEXT: a = 2;248#ifdef OMP52249#pragma omp target parallel for simd private(argc, b), firstprivate(argv, c), lastprivate(d, f) collapse(2) schedule(auto) ordered if (target: argc) num_threads(a) default(shared) shared(e) reduction(+ : h) linear(a: step(-5))250#else251#pragma omp target parallel for simd private(argc, b), firstprivate(argv, c), lastprivate(d, f) collapse(2) schedule(auto) ordered if (target: argc) num_threads(a) default(shared) shared(e) reduction(+ : h) linear(a:-5)252#endif253 for (int i = 0; i < 10; ++i)254 for (int j = 0; j < 10; ++j)255 foo();256 // CHECK: #pragma omp target parallel for simd private(argc,b) firstprivate(argv,c) lastprivate(d,f) collapse(2) schedule(auto) ordered if(target: argc) num_threads(a) default(shared) shared(e) reduction(+: h) linear(a: step(-5))257 // CHECK-NEXT: for (int i = 0; i < 10; ++i)258 // CHECK-NEXT: for (int j = 0; j < 10; ++j)259 // CHECK-NEXT: foo();260 261#pragma omp target parallel for simd default(none), private(argc,b) firstprivate(argv) shared (d) if (parallel:argc > 0) num_threads(5) proc_bind(master) reduction(+:c, arr1[argc]) reduction(max:e, arr[:5][0:10])262 for (int i = 0; i < 2; ++i) {}263 // CHECK: #pragma omp target parallel for simd default(none) private(argc,b) firstprivate(argv) shared(d) if(parallel: argc > 0) num_threads(5) proc_bind(master) reduction(+: c,arr1[argc]) reduction(max: e,arr[:5][0:10])264 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {265 // CHECK-NEXT: }266 267#pragma omp target parallel for simd if (5) num_threads(s) proc_bind(close) reduction(^:e, f, arr[0:5][:argc]) reduction(&& : h)268 for (int i = 0; i < 2; ++i) {}269 // CHECK: #pragma omp target parallel for simd if(5) num_threads(s) proc_bind(close) reduction(^: e,f,arr[0:5][:argc]) reduction(&&: h)270 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {271 // CHECK-NEXT: }272 273#pragma omp target parallel for simd if (target:argc > 0)274 for (int i = 0; i < 2; ++i) {}275 // CHECK: #pragma omp target parallel for simd if(target: argc > 0)276 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {277 // CHECK-NEXT: }278 279#if defined(OMP51) || defined(OMP52)280#pragma omp target parallel for simd if (parallel:argc > 0)281#elif OMP5282#pragma omp target parallel for simd if (parallel:argc > 0) if(simd: argc)283#else284#pragma omp target parallel for simd if (parallel:argc > 0)285#endif // OMP51286 for (int i = 0; i < 2; ++i) {}287 // OMP45: #pragma omp target parallel for simd if(parallel: argc > 0)288 // OMP50: #pragma omp target parallel for simd if(parallel: argc > 0) if(simd: argc)289 // OMP51: #pragma omp target parallel for simd if(parallel: argc > 0)290 // OMP52: #pragma omp target parallel for simd if(parallel: argc > 0)291 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {292 // CHECK-NEXT: }293 294#pragma omp target parallel for simd if (5)295 for (int i = 0; i < 2; ++i) {}296 // CHECK: #pragma omp target parallel for simd if(5)297 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {298 // CHECK-NEXT: }299 300#pragma omp target parallel for simd map(i)301 for (int i = 0; i < 2; ++i) {}302 // CHECK: #pragma omp target parallel for simd map(tofrom: i)303 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {304 // CHECK-NEXT: }305 306#pragma omp target parallel for simd map(arr1[0:10], i)307 for (int i = 0; i < 2; ++i) {}308 // CHECK: #pragma omp target parallel for simd map(tofrom: arr1[0:10],i)309 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {310 // CHECK-NEXT: }311 312#pragma omp target parallel for simd map(to: i) map(from: j)313 for (int i = 0; i < 2; ++i) {}314 // CHECK: #pragma omp target parallel for simd map(to: i) map(from: j)315 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {316 // CHECK-NEXT: }317 318#pragma omp target parallel for simd map(always,alloc: i)319 for (int i = 0; i < 2; ++i) {}320 // CHECK: #pragma omp target parallel for simd map(always,alloc: i)321 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {322 // CHECK-NEXT: }323 324#pragma omp target parallel for simd nowait325 for (int i = 0; i < 2; ++i) {}326 // CHECK: #pragma omp target parallel for simd nowait327 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {328 // CHECK-NEXT: }329 330#pragma omp target parallel for simd depend(in : argc, arr[i:argc], arr1[:])331 for (int i = 0; i < 2; ++i) {}332 // CHECK: #pragma omp target parallel for simd depend(in : argc,arr[i:argc],arr1[:])333 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {334 // CHECK-NEXT: }335 336#pragma omp target parallel for simd defaultmap(tofrom: scalar)337 for (int i = 0; i < 2; ++i) {}338 // CHECK: #pragma omp target parallel for simd defaultmap(tofrom: scalar)339 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {340 // CHECK-NEXT: }341 342#pragma omp target parallel for simd safelen(clen-1)343 for (int i = 0; i < 2; ++i) {}344 // CHECK: #pragma omp target parallel for simd safelen(clen - 1)345 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {346 // CHECK-NEXT: }347 348#pragma omp target parallel for simd simdlen(clen-1)349 for (int i = 0; i < 2; ++i) {}350 // CHECK: #pragma omp target parallel for simd simdlen(clen - 1)351 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {352 // CHECK-NEXT: }353 354#pragma omp target parallel for simd aligned(arr1:4)355 for (int i = 0; i < 2; ++i) {}356 // CHECK: #pragma omp target parallel for simd aligned(arr1: 4)357 // CHECK-NEXT: for (int i = 0; i < 2; ++i) {358 // CHECK-NEXT: }359 360 return (tmain<int, 5>(argc, &argc));361}362 363#endif364