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 // CHECK-DAG: @globals = global %struct.S zeroinitializer, 21 // CHECK-DAG: @llvm.used = appending global [1 x i8*] [i8* bitcast (void ()* @__omp_offloading__{{.+}}_globals_l[[@LINE+41]]_ctor to i8*)], section "llvm.metadata" 22 23 // CHECK-DAG: define {{.*}}i32 @{{.*}}{{foo|bar|baz2|baz3|FA|f_method}}{{.*}}() 24 // CHECK-DAG: define {{.*}}void @{{.*}}TemplateClass{{.*}}(%class.TemplateClass* %{{.*}}) 25 // CHECK-DAG: define {{.*}}i32 @{{.*}}TemplateClass{{.*}}f_method{{.*}}(%class.TemplateClass* %{{.*}}) 26 // CHECK-DAG: define {{.*}}void @__omp_offloading__{{.*}}_globals_l[[@LINE+36]]_ctor() 27 28 #ifndef HEADER 29 #define HEADER 30 31 template <typename T> 32 class TemplateClass { 33 T a; 34 public: 35 TemplateClass() {} 36 T f_method() const { return a; } 37 }; 38 39 int foo(); 40 41 int baz1(); 42 43 int baz2(); 44 45 int baz4() { return 5; } 46 47 template <typename T> 48 T FA() { 49 TemplateClass<T> s; 50 return s.f_method(); 51 } 52 53 #pragma omp declare target 54 struct S { 55 int a; 56 S(int a) : a(a) {} 57 }; 58 59 int foo() { return 0; } 60 int b = 15; 61 int d; 62 S globals(d); 63 #pragma omp end declare target 64 int c; 65 66 int bar() { return 1 + foo() + bar() + baz1() + baz2(); } 67 68 int maini1() { 69 int a; 70 static long aa = 32; 71 // CHECK-DAG: define weak void @__omp_offloading_{{.*}}maini1{{.*}}_l[[@LINE+1]](i32* dereferenceable{{.*}}, i64 {{.*}}, i64 {{.*}}) 72 #pragma omp target map(tofrom \ 73 : a, b) 74 { 75 S s(a); 76 static long aaa = 23; 77 a = foo() + bar() + b + c + d + aa + aaa + FA<int>(); 78 } 79 return baz4(); 80 } 81 82 int baz3() { return 2 + baz2(); } 83 int baz2() { 84 // CHECK-DAG: define weak void @__omp_offloading_{{.*}}baz2{{.*}}_l[[@LINE+1]](i64 {{.*}}) 85 #pragma omp target parallel 86 ++c; 87 return 2 + baz3(); 88 } 89 90 // CHECK-NOT: define {{.*}}{{baz1|baz4|maini1}} 91 #endif // HEADER 92