1 // RUN: %clang_cc1 -verify -fopenmp -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple x86_64-unknown-unknown -emit-llvm %s -o - | FileCheck %s
2 // RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -std=c++11 -triple x86_64-unknown-unknown -emit-pch -o %t %s
3 // RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple x86_64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck %s
4 
5 // RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple x86_64-unknown-unknown -emit-llvm %s -o - | FileCheck --check-prefix SIMD-ONLY0 %s
6 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -std=c++11 -triple x86_64-unknown-unknown -emit-pch -o %t %s
7 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple x86_64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck --check-prefix SIMD-ONLY0 %s
8 // SIMD-ONLY0-NOT: {{__kmpc|__tgt}}
9 
10 // RUN: %clang_cc1 -verify -fopenmp -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple x86_64-unknown-unknown -emit-llvm %s -o - | FileCheck %s
11 // RUN: %clang_cc1 -fopenmp -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -std=c++11 -triple x86_64-unknown-unknown -emit-pch -o %t %s
12 // RUN: %clang_cc1 -fopenmp -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple x86_64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck %s
13 
14 // RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple x86_64-unknown-unknown -emit-llvm %s -o - | FileCheck --check-prefix SIMD-ONLY0 %s
15 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -std=c++11 -triple x86_64-unknown-unknown -emit-pch -o %t %s
16 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple x86_64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck --check-prefix SIMD-ONLY0 %s
17 // SIMD-ONLY0-NOT: {{__kmpc|__tgt}}
18 
19 // RUN: %clang_cc1 -verify -fopenmp -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple aarch64-unknown-unknown -emit-llvm %s -o - | FileCheck %s
20 // RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -std=c++11 -triple aarch64-unknown-unknown -emit-pch -o %t %s
21 // RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple aarch64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck %s
22 
23 // RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple aarch64-unknown-unknown -emit-llvm %s -o - | FileCheck --check-prefix SIMD-ONLY0 %s
24 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -std=c++11 -triple aarch64-unknown-unknown -emit-pch -o %t %s
25 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-version=45 -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple aarch64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck --check-prefix SIMD-ONLY0 %s
26 // SIMD-ONLY0-NOT: {{__kmpc|__tgt}}
27 
28 // RUN: %clang_cc1 -verify -fopenmp -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple aarch64-unknown-unknown -emit-llvm %s -o - | FileCheck %s
29 // RUN: %clang_cc1 -fopenmp -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -std=c++11 -triple aarch64-unknown-unknown -emit-pch -o %t %s
30 // RUN: %clang_cc1 -fopenmp -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple aarch64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck %s
31 
32 // RUN: %clang_cc1 -verify -fopenmp-simd -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple aarch64-unknown-unknown -emit-llvm %s -o - | FileCheck --check-prefix SIMD-ONLY0 %s
33 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -std=c++11 -triple aarch64-unknown-unknown -emit-pch -o %t %s
34 // RUN: %clang_cc1 -fopenmp-simd -fopenmp-targets=powerpc64le-ibm-linux-gnu -x c++ -triple aarch64-unknown-unknown -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck --check-prefix SIMD-ONLY0 %s
35 // SIMD-ONLY0-NOT: {{__kmpc|__tgt}}
36 
37 // expected-no-diagnostics
38 #ifndef HEADER
39 #define HEADER
40 
41 void fn1();
42 void fn2();
43 void fn3();
44 void fn4();
45 void fn5();
46 void fn6();
47 
48 int Arg;
49 
50 // CHECK-LABEL: define {{.*}}void @{{.+}}gtid_test
51 void gtid_test() {
52 #pragma omp target
53 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(
54 // CHECK: call void [[OFFLOADING_FUN_0:@.+]](
55 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(
56 // CHECK: call void [[OFFLOADING_FUN_1:@.+]](
57 #pragma omp teams distribute parallel for
58   for(int i = 0 ; i < 100; i++) {}
59   // CHECK: define internal void [[OFFLOADING_FUN_0]](
60   // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 0, {{.+}}* [[OMP_TEAMS_OUTLINED_0:@.+]] to {{.+}})
61   // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_0]](
62   // CHECK: call void @__kmpc_for_static_init_4(
63   // CHECK:  call void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, {{.+}}* [[OMP_OUTLINED_0:@.+]] to void
64   // CHECK: call void @__kmpc_for_static_fini(
65 
66   // CHECK: define{{.+}} void [[OMP_OUTLINED_0]](
67   // CHECK: call void @__kmpc_for_static_init_4(
68   // CHECK: call void @__kmpc_for_static_fini(
69   // CHECK: ret
70 #pragma omp target
71 #pragma omp teams distribute parallel for if (parallel: false)
72   for(int i = 0 ; i < 100; i++) {
73   // CHECK: define internal void [[OFFLOADING_FUN_1]](
74   // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 0, {{.+}}* [[OMP_TEAMS_OUTLINED_1:@.+]] to {{.+}})
75   // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_1]](
76   // CHECK: call void @__kmpc_for_static_init_4(
77   // CHECK: call void @__kmpc_serialized_parallel(
78   // CHECK: call void [[OMP_OUTLINED_1:@.+]](
79   // CHECK: call void @__kmpc_end_serialized_parallel(
80   // CHECK: call void @__kmpc_for_static_fini(
81   // CHECK: define{{.+}} void [[OMP_OUTLINED_1]](
82   // CHECK: call void @__kmpc_for_static_init_4(
83   // CHECK: call void @{{.+}}gtid_test
84   // CHECK: call void @__kmpc_for_static_fini(
85   // CHECK: ret
86     gtid_test();
87   }
88 }
89 
90 
91 template <typename T>
92 int tmain(T Arg) {
93 #pragma omp target
94 #pragma omp teams distribute parallel for if (true)
95   for(int i = 0 ; i < 100; i++) {
96     fn1();
97   }
98 #pragma omp target
99 #pragma omp teams distribute parallel for if (false)
100   for(int i = 0 ; i < 100; i++) {
101     fn2();
102   }
103 #pragma omp target
104 #pragma omp teams distribute parallel for if (parallel: Arg)
105   for(int i = 0 ; i < 100; i++) {
106     fn3();
107   }
108   return 0;
109 }
110 
111 // CHECK-LABEL: define {{.*}}i{{[0-9]+}} @main()
112 int main() {
113 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(
114 // CHECK: call void [[OFFLOADING_FUN_0:@.+]](
115 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(
116 // CHECK: call void [[OFFLOADING_FUN_1:@.+]](
117 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(
118 // CHECK: call void [[OFFLOADING_FUN_2:@.+]](
119 // CHECK: = call {{.*}}i{{.+}} @{{.+}}tmain
120 #pragma omp target
121 #pragma omp teams distribute parallel for if (true)
122   for(int i = 0 ; i < 100; i++) {
123     // CHECK: define internal void [[OFFLOADING_FUN_0]](
124     // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 0, {{.+}}* [[OMP_TEAMS_OUTLINED_0:@.+]] to {{.+}})
125     // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_0]](
126 
127     // CHECK: call void @__kmpc_for_static_init_4(
128     // CHECK: call void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, {{.+}}* [[OMP_OUTLINED_2:@.+]] to void
129     // CHECK: call void @__kmpc_for_static_fini(
130     // CHECK: define{{.+}} void [[OMP_OUTLINED_2]](
131     // CHECK: call void @__kmpc_for_static_init_4(
132     // CHECK: call {{.*}}void @{{.+}}fn4
133     // CHECK: call void @__kmpc_for_static_fini(
134 
135     fn4();
136   }
137 
138 #pragma omp target
139 #pragma omp teams distribute parallel for if (false)
140   for(int i = 0 ; i < 100; i++) {
141     // CHECK: define internal void [[OFFLOADING_FUN_1]](
142     // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 0, {{.+}}* [[OMP_TEAMS_OUTLINED_1:@.+]] to {{.+}})
143     // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_1]](
144 
145     // CHECK: call void @__kmpc_for_static_init_4(
146     // CHECK: call void @__kmpc_serialized_parallel(
147     // CHECK: call void [[OMP_OUTLINED_3:@.+]](
148     // CHECK: call void @__kmpc_end_serialized_parallel(
149     // CHECK: call void @__kmpc_for_static_fini(
150 
151     // CHECK: define{{.+}} void [[OMP_OUTLINED_3]](
152     // CHECK: call void @__kmpc_for_static_init_4(
153     // CHECK: call {{.*}}void @{{.+}}fn5
154     // CHECK: call void @__kmpc_for_static_fini(
155     fn5();
156   }
157 
158 #pragma omp target
159 #pragma omp teams distribute parallel for if (Arg)
160   for(int i = 0 ; i < 100; i++) {
161     // CHECK: define internal void [[OFFLOADING_FUN_2]](
162     // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 1, {{.+}}* [[OMP_TEAMS_OUTLINED_2:@.+]] to {{.+}})
163     // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_2]](
164 
165     // CHECK: call void @__kmpc_for_static_init_4(
166     // CHECK: call void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, {{.+}}* [[OMP_OUTLINED_4:@.+]] to void
167     // CHECK: call void @__kmpc_serialized_parallel(
168     // CHECK: call void [[OMP_OUTLINED_4:@.+]](
169     // CHECK: call void @__kmpc_end_serialized_parallel(
170     // CHECK: call void @__kmpc_for_static_fini(
171 
172     // CHECK: define{{.+}} void [[OMP_OUTLINED_4]](
173     // CHECK: call void @__kmpc_for_static_init_4(
174     // CHECK: call {{.*}}void @{{.+}}fn6
175     // CHECK: call void @__kmpc_for_static_fini(
176     fn6();
177   }
178 
179   return tmain(Arg);
180 }
181 
182 // CHECK-LABEL: define {{.+}} @{{.+}}tmain
183 
184 // CHECK: call void @__kmpc_for_static_init_4(
185 // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, void {{.+}}* [[T_OUTLINE_FUN_1:@.+]] to void
186 // CHECK: call void @__kmpc_for_static_fini(
187 
188 // CHECK: define internal {{.*}}void [[T_OUTLINE_FUN_1]]
189 // CHECK: call void @__kmpc_for_static_init_4(
190 // CHECK: call {{.*}}void @{{.+}}fn1
191 // CHECK: call void @__kmpc_for_static_fini(
192 // CHECK: ret void
193 
194 // CHECK: call void @__kmpc_for_static_init_4(
195 // CHECK: call {{.*}}void @__kmpc_serialized_parallel(
196 // CHECK: call void [[T_OUTLINE_FUN_2:@.+]](
197 // CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(
198 // CHECK: call void @__kmpc_for_static_fini(
199 
200 // CHECK: define internal {{.*}}void [[T_OUTLINE_FUN_2]]
201 // CHECK: call void @__kmpc_for_static_init_4(
202 // CHECK: call {{.*}}void @{{.+}}fn2
203 // CHECK: call void @__kmpc_for_static_fini(
204 // CHECK: ret void
205 
206 // CHECK: call void @__kmpc_for_static_init_4(
207 // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, void {{.+}}* [[T_OUTLINE_FUN_3:@.+]] to void
208 // CHECK: call {{.*}}void @__kmpc_serialized_parallel(
209 // call void [[T_OUTLINE_FUN_3:@.+]](
210 // CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(
211 
212 // CHECK: define internal {{.*}}void [[T_OUTLINE_FUN_3]]
213 // CHECK: call void @__kmpc_for_static_init_4(
214 // CHECK: call {{.*}}void @{{.+}}fn3
215 // CHECK: call void @__kmpc_for_static_fini(
216 // CHECK: ret void
217 #endif
218