1 // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=powerpc64le-ibm-linux-gnu -emit-llvm-bc %s -o %t-ppc-host.bc 2 // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=powerpc64le-ibm-linux-gnu -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -o - | FileCheck %s 3 // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=powerpc64le-ibm-linux-gnu -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -emit-pch -o %t 4 // RUN: %clang_cc1 -verify -fopenmp -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=powerpc64le-ibm-linux-gnu -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -include-pch %t -o - | FileCheck %s 5 6 // RUN: %clang_cc1 -verify -fopenmp-simd -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=powerpc64le-ibm-linux-gnu -emit-llvm-bc %s -o %t-ppc-host.bc 7 // RUN: %clang_cc1 -verify -fopenmp-simd -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=powerpc64le-ibm-linux-gnu -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -o -| FileCheck %s --check-prefix SIMD-ONLY 8 // RUN: %clang_cc1 -verify -fopenmp-simd -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=powerpc64le-ibm-linux-gnu -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -emit-pch -o %t 9 // RUN: %clang_cc1 -verify -fopenmp-simd -x c++ -triple powerpc64le-unknown-unknown -fopenmp-targets=powerpc64le-ibm-linux-gnu -emit-llvm %s -fopenmp-is-device -fopenmp-host-ir-file-path %t-ppc-host.bc -include-pch %t -verify -o - | FileCheck %s --check-prefix SIMD-ONLY 10 11 // expected-no-diagnostics 12 13 // SIMD-ONLY-NOT: {{__kmpc|__tgt}} 14 15 // CHECK-NOT: define {{.*}}{{baz1|baz4|maini1}} 16 // CHECK-DAG: @{{.*}}maini1{{.*}}aaa = internal global i64 23, 17 // CHECK-DAG: @b = global i32 15, 18 // CHECK-DAG: @d = global i32 0, 19 // CHECK-DAG: @c = external global i32, 20 21 // CHECK-DAG: define {{.*}}i32 @{{.*}}{{foo|bar|baz2|baz3}}{{.*}}() 22 23 #ifndef HEADER 24 #define HEADER 25 26 int foo(); 27 28 int baz1(); 29 30 int baz2(); 31 32 int baz4() { return 5; } 33 34 #pragma omp declare target 35 int foo() { return 0; } 36 int b = 15; 37 int d; 38 #pragma omp end declare target 39 int c; 40 41 int bar() { return 1 + foo() + bar() + baz1() + baz2(); } 42 43 int maini1() { 44 int a; 45 static long aa = 32; 46 // CHECK-DAG: define void @__omp_offloading_{{.*}}maini1{{.*}}_l[[@LINE+1]](i32* dereferenceable{{.*}}, i64 {{.*}}, i64 {{.*}}) 47 #pragma omp target map(tofrom \ 48 : a) 49 { 50 static long aaa = 23; 51 a = foo() + bar() + b + c + d + aa + aaa; 52 } 53 return baz4(); 54 } 55 56 int baz3(); 57 int baz2() { 58 // CHECK-DAG: define void @__omp_offloading_{{.*}}baz2{{.*}}_l[[@LINE+1]](i64 {{.*}}) 59 #pragma omp target 60 ++c; 61 return 2 + baz3(); 62 } 63 int baz3() { return 2 + baz2(); } 64 65 // CHECK-NOT: define {{.*}}{{baz1|baz4|maini1}} 66 #endif // HEADER 67