blob: 9ecf57211f85376a4b3ba1e89b372016f89df1b0 [file] [log] [blame]
Pirama Arumuga Nainarb6d69932015-07-01 12:25:36 -07001// RUN: %clang_cc1 -verify -fopenmp -x c++ -triple %itanium_abi_triple -emit-llvm %s -o - | FileCheck %s
2// RUN: %clang_cc1 -fopenmp -x c++ -std=c++11 -triple %itanium_abi_triple -emit-pch -o %t %s
3// RUN: %clang_cc1 -fopenmp -x c++ -triple %itanium_abi_triple -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck --check-prefix=CHECK %s
Stephen Hines176edba2014-12-01 14:53:08 -08004// expected-no-diagnostics
5#ifndef HEADER
6#define HEADER
7
8void fn1();
9void fn2();
10void fn3();
11void fn4();
12void fn5();
13void fn6();
14
15int Arg;
16
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080017// CHECK-LABEL: define {{.*}}void @{{.+}}gtid_test
Stephen Hines176edba2014-12-01 14:53:08 -080018void gtid_test() {
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080019// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, {{.+}}* [[GTID_TEST_REGION1:@.+]] to void
Stephen Hines176edba2014-12-01 14:53:08 -080020#pragma omp parallel
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080021#pragma omp parallel if (parallel: false)
Stephen Hines176edba2014-12-01 14:53:08 -080022 gtid_test();
23// CHECK: ret void
24}
25
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080026// CHECK: define internal {{.*}}void [[GTID_TEST_REGION1]](i{{.+}}* noalias [[GTID_PARAM:%.+]], i32* noalias
Stephen Hines176edba2014-12-01 14:53:08 -080027// CHECK: store i{{[0-9]+}}* [[GTID_PARAM]], i{{[0-9]+}}** [[GTID_ADDR_REF:%.+]],
Pirama Arumuga Nainar3ea9e332015-04-08 08:57:32 -070028// CHECK: [[GTID_ADDR:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[GTID_ADDR_REF]]
29// CHECK: [[GTID:%.+]] = load i{{[0-9]+}}, i{{[0-9]+}}* [[GTID_ADDR]]
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080030// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i{{.+}} [[GTID]])
Pirama Arumuga Nainar3ea9e332015-04-08 08:57:32 -070031// CHECK: [[GTID_ADDR:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[GTID_ADDR_REF]]
Stephen Hines176edba2014-12-01 14:53:08 -080032// CHECK: call void [[GTID_TEST_REGION2:@.+]](i{{[0-9]+}}* [[GTID_ADDR]]
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080033// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i{{.+}} [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -080034// CHECK: ret void
35
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080036// CHECK: define internal {{.*}}void [[GTID_TEST_REGION2]](
37// CHECK: call {{.*}}void @{{.+}}gtid_test
Stephen Hines176edba2014-12-01 14:53:08 -080038// CHECK: ret void
39
40template <typename T>
41int tmain(T Arg) {
42#pragma omp parallel if (true)
43 fn1();
44#pragma omp parallel if (false)
45 fn2();
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080046#pragma omp parallel if (parallel: Arg)
Stephen Hines176edba2014-12-01 14:53:08 -080047 fn3();
48 return 0;
49}
50
51// CHECK-LABEL: define {{.*}}i{{[0-9]+}} @main()
52int main() {
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080053// CHECK: [[GTID:%.+]] = call {{.*}}i32 @__kmpc_global_thread_num(
54// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, void {{.+}}* [[CAP_FN4:@.+]] to void
Stephen Hines176edba2014-12-01 14:53:08 -080055#pragma omp parallel if (true)
56 fn4();
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080057// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -080058// CHECK: store i32 [[GTID]], i32* [[GTID_ADDR:%.+]],
59// CHECK: call void [[CAP_FN5:@.+]](i32* [[GTID_ADDR]],
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080060// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -080061#pragma omp parallel if (false)
62 fn5();
63
64// CHECK: br i1 %{{.+}}, label %[[OMP_THEN:.+]], label %[[OMP_ELSE:.+]]
65// CHECK: [[OMP_THEN]]
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080066// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, void {{.+}}* [[CAP_FN6:@.+]] to void
Stephen Hines176edba2014-12-01 14:53:08 -080067// CHECK: br label %[[OMP_END:.+]]
68// CHECK: [[OMP_ELSE]]
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080069// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -080070// CHECK: store i32 [[GTID]], i32* [[GTID_ADDR:%.+]],
71// CHECK: call void [[CAP_FN6]](i32* [[GTID_ADDR]],
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080072// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -080073// CHECK: br label %[[OMP_END]]
74// CHECK: [[OMP_END]]
75#pragma omp parallel if (Arg)
76 fn6();
77 // CHECK: = call {{.*}}i{{.+}} @{{.+}}tmain
78 return tmain(Arg);
79}
80
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080081// CHECK: define internal {{.*}}void [[CAP_FN4]]
82// CHECK: call {{.*}}void @{{.+}}fn4
Stephen Hines176edba2014-12-01 14:53:08 -080083// CHECK: ret void
84
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080085// CHECK: define internal {{.*}}void [[CAP_FN5]]
86// CHECK: call {{.*}}void @{{.+}}fn5
Stephen Hines176edba2014-12-01 14:53:08 -080087// CHECK: ret void
88
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080089// CHECK: define internal {{.*}}void [[CAP_FN6]]
90// CHECK: call {{.*}}void @{{.+}}fn6
Stephen Hines176edba2014-12-01 14:53:08 -080091// CHECK: ret void
92
93// CHECK-LABEL: define {{.+}} @{{.+}}tmain
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080094// CHECK: [[GTID:%.+]] = call {{.*}}i32 @__kmpc_global_thread_num(
95// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, void {{.+}}* [[CAP_FN1:@.+]] to void
96// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -080097// CHECK: store i32 [[GTID]], i32* [[GTID_ADDR:%.+]],
98// CHECK: call void [[CAP_FN2:@.+]](i32* [[GTID_ADDR]],
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -080099// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -0800100// CHECK: br i1 %{{.+}}, label %[[OMP_THEN:.+]], label %[[OMP_ELSE:.+]]
101// CHECK: [[OMP_THEN]]
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -0800102// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, void {{.+}}* [[CAP_FN3:@.+]] to void
Stephen Hines176edba2014-12-01 14:53:08 -0800103// CHECK: br label %[[OMP_END:.+]]
104// CHECK: [[OMP_ELSE]]
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -0800105// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -0800106// CHECK: store i32 [[GTID]], i32* [[GTID_ADDR:%.+]],
107// CHECK: call void [[CAP_FN3]](i32* [[GTID_ADDR]],
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -0800108// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Stephen Hines176edba2014-12-01 14:53:08 -0800109// CHECK: br label %[[OMP_END]]
110// CHECK: [[OMP_END]]
111
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -0800112// CHECK: define internal {{.*}}void [[CAP_FN1]]
113// CHECK: call {{.*}}void @{{.+}}fn1
Stephen Hines176edba2014-12-01 14:53:08 -0800114// CHECK: ret void
115
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -0800116// CHECK: define internal {{.*}}void [[CAP_FN2]]
117// CHECK: call {{.*}}void @{{.+}}fn2
Stephen Hines176edba2014-12-01 14:53:08 -0800118// CHECK: ret void
119
Pirama Arumuga Nainar87d948e2016-03-03 15:49:35 -0800120// CHECK: define internal {{.*}}void [[CAP_FN3]]
121// CHECK: call {{.*}}void @{{.+}}fn3
Stephen Hines176edba2014-12-01 14:53:08 -0800122// CHECK: ret void
123
124#endif