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