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 #pragma omp teams
54 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(%struct.ident_t* @{{.+}},
55 // CHECK: call void [[OFFLOADING_FUN_0:@.+]](
56 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(%struct.ident_t* @{{.+}},
57 // CHECK: call void [[OFFLOADING_FUN_1:@.+]](
58 #pragma omp distribute parallel for
59   for(int i = 0 ; i < 100; i++) {}
60   // CHECK: define internal void [[OFFLOADING_FUN_0]](
61   // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 0, {{.+}}* [[OMP_TEAMS_OUTLINED_0:@.+]] to {{.+}})
62   // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_0]](
63   // CHECK: call void @__kmpc_for_static_init_4(
64   // CHECK:  call void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, {{.+}}* [[OMP_OUTLINED_0:@.+]] to void
65   // CHECK: call void @__kmpc_for_static_fini(
66 
67   // CHECK: define{{.+}} void [[OMP_OUTLINED_0]](
68   // CHECK: call void @__kmpc_for_static_init_4(
69   // CHECK: call void @__kmpc_for_static_fini(
70   // CHECK: ret
71 #pragma omp target
72 #pragma omp teams
73 #pragma omp distribute parallel for if (parallel: false)
74   for(int i = 0 ; i < 100; i++) {
75   // CHECK: define internal void [[OFFLOADING_FUN_1]](
76   // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 0, {{.+}}* [[OMP_TEAMS_OUTLINED_1:@.+]] to {{.+}})
77   // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_1]](
78   // CHECK: call void @__kmpc_for_static_init_4(
79   // CHECK: call void @__kmpc_serialized_parallel(
80   // CHECK: call void [[OMP_OUTLINED_1:@.+]](
81   // CHECK: call void @__kmpc_end_serialized_parallel(
82   // CHECK: call void @__kmpc_for_static_fini(
83   // CHECK: define{{.+}} void [[OMP_OUTLINED_1]](
84   // CHECK: call void @__kmpc_for_static_init_4(
85   // CHECK: call void @{{.+}}gtid_test
86   // CHECK: call void @__kmpc_for_static_fini(
87   // CHECK: ret
88     gtid_test();
89   }
90 }
91 
92 
93 template <typename T>
94 int tmain(T Arg) {
95 #pragma omp target
96 #pragma omp teams
97 #pragma omp distribute parallel for if (true)
98   for(int i = 0 ; i < 100; i++) {
99     fn1();
100   }
101 #pragma omp target
102 #pragma omp teams
103 #pragma omp distribute parallel for if (false)
104   for(int i = 0 ; i < 100; i++) {
105     fn2();
106   }
107 #pragma omp target
108 #pragma omp teams
109 #pragma omp distribute parallel for if (parallel: Arg)
110   for(int i = 0 ; i < 100; i++) {
111     fn3();
112   }
113   return 0;
114 }
115 
116 // CHECK-LABEL: define {{.*}}i{{[0-9]+}} @main()
117 int main() {
118 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(%struct.ident_t* @{{.+}},
119 // CHECK: call void [[OFFLOADING_FUN_0:@.+]](
120 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(%struct.ident_t* @{{.+}},
121 // CHECK: call void [[OFFLOADING_FUN_1:@.+]](
122 // CHECK: call i{{[0-9]+}} @__tgt_target_teams_mapper(%struct.ident_t* @{{.+}},
123 // CHECK: call void [[OFFLOADING_FUN_2:@.+]](
124 // CHECK: = call {{.*}}i{{.+}} @{{.+}}tmain
125 #pragma omp target
126 #pragma omp teams
127 #pragma omp distribute parallel for if (true)
128   for(int i = 0 ; i < 100; i++) {
129     // CHECK: define internal void [[OFFLOADING_FUN_0]](
130     // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 0, {{.+}}* [[OMP_TEAMS_OUTLINED_0:@.+]] to {{.+}})
131     // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_0]](
132 
133     // CHECK: call void @__kmpc_for_static_init_4(
134     // CHECK: call void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, {{.+}}* [[OMP_OUTLINED_2:@.+]] to void
135     // CHECK: call void @__kmpc_for_static_fini(
136     // CHECK: define{{.+}} void [[OMP_OUTLINED_2]](
137     // CHECK: call void @__kmpc_for_static_init_4(
138     // CHECK: call {{.*}}void @{{.+}}fn4
139     // CHECK: call void @__kmpc_for_static_fini(
140 
141     fn4();
142   }
143 
144 #pragma omp target
145 #pragma omp teams
146 #pragma omp distribute parallel for if (false)
147   for(int i = 0 ; i < 100; i++) {
148     // CHECK: define internal void [[OFFLOADING_FUN_1]](
149     // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 0, {{.+}}* [[OMP_TEAMS_OUTLINED_1:@.+]] to {{.+}})
150     // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_1]](
151 
152     // CHECK: call void @__kmpc_for_static_init_4(
153     // CHECK: call void @__kmpc_serialized_parallel(
154     // CHECK: call void [[OMP_OUTLINED_3:@.+]](
155     // CHECK: call void @__kmpc_end_serialized_parallel(
156     // CHECK: call void @__kmpc_for_static_fini(
157 
158     // CHECK: define{{.+}} void [[OMP_OUTLINED_3]](
159     // CHECK: call void @__kmpc_for_static_init_4(
160     // CHECK: call {{.*}}void @{{.+}}fn5
161     // CHECK: call void @__kmpc_for_static_fini(
162     fn5();
163   }
164 
165 #pragma omp target
166 #pragma omp teams
167 #pragma omp distribute parallel for if (Arg)
168   for(int i = 0 ; i < 100; i++) {
169     // CHECK: define internal void [[OFFLOADING_FUN_2]](
170     // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_teams({{.+}}, i32 1, {{.+}}* [[OMP_TEAMS_OUTLINED_2:@.+]] to {{.+}})
171     // CHECK: define{{.+}} void [[OMP_TEAMS_OUTLINED_2]](
172 
173     // CHECK: call void @__kmpc_for_static_init_4(
174     // CHECK: call void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, {{.+}}* [[OMP_OUTLINED_4:@.+]] to void
175     // CHECK: call void @__kmpc_serialized_parallel(
176     // CHECK: call void [[OMP_OUTLINED_4:@.+]](
177     // CHECK: call void @__kmpc_end_serialized_parallel(
178     // CHECK: call void @__kmpc_for_static_fini(
179 
180     // CHECK: define{{.+}} void [[OMP_OUTLINED_4]](
181     // CHECK: call void @__kmpc_for_static_init_4(
182     // CHECK: call {{.*}}void @{{.+}}fn6
183     // CHECK: call void @__kmpc_for_static_fini(
184     fn6();
185   }
186 
187   return tmain(Arg);
188 }
189 
190 // CHECK-LABEL: define {{.+}} @{{.+}}tmain
191 
192 // CHECK: call void @__kmpc_for_static_init_4(
193 // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, void {{.+}}* [[T_OUTLINE_FUN_1:@.+]] to void
194 // CHECK: call void @__kmpc_for_static_fini(
195 
196 // CHECK: define internal {{.*}}void [[T_OUTLINE_FUN_1]]
197 // CHECK: call void @__kmpc_for_static_init_4(
198 // CHECK: call {{.*}}void @{{.+}}fn1
199 // CHECK: call void @__kmpc_for_static_fini(
200 // CHECK: ret void
201 
202 // CHECK: call void @__kmpc_for_static_init_4(
203 // CHECK: call {{.*}}void @__kmpc_serialized_parallel(
204 // CHECK: call void [[T_OUTLINE_FUN_2:@.+]](
205 // CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(
206 // CHECK: call void @__kmpc_for_static_fini(
207 
208 // CHECK: define internal {{.*}}void [[T_OUTLINE_FUN_2]]
209 // CHECK: call void @__kmpc_for_static_init_4(
210 // CHECK: call {{.*}}void @{{.+}}fn2
211 // CHECK: call void @__kmpc_for_static_fini(
212 // CHECK: ret void
213 
214 // CHECK: call void @__kmpc_for_static_init_4(
215 // CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 2, void {{.+}}* [[T_OUTLINE_FUN_3:@.+]] to void
216 // CHECK: call {{.*}}void @__kmpc_serialized_parallel(
217 // call void [[T_OUTLINE_FUN_3:@.+]](
218 // CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(
219 
220 // CHECK: define internal {{.*}}void [[T_OUTLINE_FUN_3]]
221 // CHECK: call void @__kmpc_for_static_init_4(
222 // CHECK: call {{.*}}void @{{.+}}fn3
223 // CHECK: call void @__kmpc_for_static_fini(
224 // CHECK: ret void
225 #endif
226