blob: 87dcf1dde943c70e05d4e70c8bbf3d59c584f34d [file] [log] [blame]
Alexey Bataev2a6de8c2016-12-20 12:10:05 +00001// RUN: %clang_cc1 -verify -fopenmp -fopenmp-version=45 -x c++ -triple %itanium_abi_triple -emit-llvm %s -o - | FileCheck %s
2// RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -x c++ -std=c++11 -triple %itanium_abi_triple -emit-pch -o %t %s
Mandeep Singh Granga16b27c2017-07-17 17:31:44 +00003// RUN: %clang_cc1 -fopenmp -fopenmp-version=45 -x c++ -triple %itanium_abi_triple -std=c++11 -include-pch %t -verify %s -emit-llvm -o - | FileCheck %s
Alexey Bataevd74d0602014-10-13 06:02:40 +00004// 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
David Blaikieea3e51d2015-06-29 17:29:50 +000017// CHECK-LABEL: define {{.*}}void @{{.+}}gtid_test
Alexey Bataevd74d0602014-10-13 06:02:40 +000018void gtid_test() {
Alexey Bataev2377fe92015-09-10 08:12:02 +000019// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, {{.+}}* [[GTID_TEST_REGION1:@.+]] to void
Alexey Bataevd74d0602014-10-13 06:02:40 +000020#pragma omp parallel
Alexey Bataev7371aa32015-09-03 08:45:56 +000021#pragma omp parallel if (parallel: false)
Alexey Bataevd74d0602014-10-13 06:02:40 +000022 gtid_test();
23// CHECK: ret void
24}
25
Alexey Bataev2377fe92015-09-10 08:12:02 +000026// CHECK: define internal {{.*}}void [[GTID_TEST_REGION1]](i{{.+}}* noalias [[GTID_PARAM:%.+]], i32* noalias
Alexey Bataevd74d0602014-10-13 06:02:40 +000027// CHECK: store i{{[0-9]+}}* [[GTID_PARAM]], i{{[0-9]+}}** [[GTID_ADDR_REF:%.+]],
David Blaikiea953f282015-02-27 21:19:58 +000028// 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]]
David Blaikieea3e51d2015-06-29 17:29:50 +000030// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i{{.+}} [[GTID]])
David Blaikiea953f282015-02-27 21:19:58 +000031// CHECK: [[GTID_ADDR:%.+]] = load i{{[0-9]+}}*, i{{[0-9]+}}** [[GTID_ADDR_REF]]
Alexey Bataevd74d0602014-10-13 06:02:40 +000032// CHECK: call void [[GTID_TEST_REGION2:@.+]](i{{[0-9]+}}* [[GTID_ADDR]]
David Blaikieea3e51d2015-06-29 17:29:50 +000033// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i{{.+}} [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +000034// CHECK: ret void
35
David Blaikieea3e51d2015-06-29 17:29:50 +000036// CHECK: define internal {{.*}}void [[GTID_TEST_REGION2]](
37// CHECK: call {{.*}}void @{{.+}}gtid_test
Alexey Bataevd74d0602014-10-13 06:02:40 +000038// 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();
Alexey Bataev7371aa32015-09-03 08:45:56 +000046#pragma omp parallel if (parallel: Arg)
Alexey Bataevd74d0602014-10-13 06:02:40 +000047 fn3();
48 return 0;
49}
50
51// CHECK-LABEL: define {{.*}}i{{[0-9]+}} @main()
52int main() {
David Blaikieea3e51d2015-06-29 17:29:50 +000053// CHECK: [[GTID:%.+]] = call {{.*}}i32 @__kmpc_global_thread_num(
Alexey Bataev2377fe92015-09-10 08:12:02 +000054// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, void {{.+}}* [[CAP_FN4:@.+]] to void
Alexey Bataevd74d0602014-10-13 06:02:40 +000055#pragma omp parallel if (true)
56 fn4();
David Blaikieea3e51d2015-06-29 17:29:50 +000057// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +000058// CHECK: store i32 [[GTID]], i32* [[GTID_ADDR:%.+]],
59// CHECK: call void [[CAP_FN5:@.+]](i32* [[GTID_ADDR]],
David Blaikieea3e51d2015-06-29 17:29:50 +000060// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +000061#pragma omp parallel if (false)
62 fn5();
63
64// CHECK: br i1 %{{.+}}, label %[[OMP_THEN:.+]], label %[[OMP_ELSE:.+]]
65// CHECK: [[OMP_THEN]]
Alexey Bataev2377fe92015-09-10 08:12:02 +000066// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, void {{.+}}* [[CAP_FN6:@.+]] to void
Alexey Bataevd74d0602014-10-13 06:02:40 +000067// CHECK: br label %[[OMP_END:.+]]
68// CHECK: [[OMP_ELSE]]
David Blaikieea3e51d2015-06-29 17:29:50 +000069// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +000070// CHECK: store i32 [[GTID]], i32* [[GTID_ADDR:%.+]],
71// CHECK: call void [[CAP_FN6]](i32* [[GTID_ADDR]],
David Blaikieea3e51d2015-06-29 17:29:50 +000072// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +000073// CHECK: br label %[[OMP_END]]
74// CHECK: [[OMP_END]]
75#pragma omp parallel if (Arg)
76 fn6();
Ulrich Weigand799c3d32014-10-13 13:49:39 +000077 // CHECK: = call {{.*}}i{{.+}} @{{.+}}tmain
Alexey Bataevd74d0602014-10-13 06:02:40 +000078 return tmain(Arg);
79}
80
David Blaikieea3e51d2015-06-29 17:29:50 +000081// CHECK: define internal {{.*}}void [[CAP_FN4]]
82// CHECK: call {{.*}}void @{{.+}}fn4
Alexey Bataevd74d0602014-10-13 06:02:40 +000083// CHECK: ret void
84
David Blaikieea3e51d2015-06-29 17:29:50 +000085// CHECK: define internal {{.*}}void [[CAP_FN5]]
86// CHECK: call {{.*}}void @{{.+}}fn5
Alexey Bataevd74d0602014-10-13 06:02:40 +000087// CHECK: ret void
88
David Blaikieea3e51d2015-06-29 17:29:50 +000089// CHECK: define internal {{.*}}void [[CAP_FN6]]
90// CHECK: call {{.*}}void @{{.+}}fn6
Alexey Bataevd74d0602014-10-13 06:02:40 +000091// CHECK: ret void
92
93// CHECK-LABEL: define {{.+}} @{{.+}}tmain
David Blaikieea3e51d2015-06-29 17:29:50 +000094// CHECK: [[GTID:%.+]] = call {{.*}}i32 @__kmpc_global_thread_num(
Alexey Bataev2377fe92015-09-10 08:12:02 +000095// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, void {{.+}}* [[CAP_FN1:@.+]] to void
David Blaikieea3e51d2015-06-29 17:29:50 +000096// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +000097// CHECK: store i32 [[GTID]], i32* [[GTID_ADDR:%.+]],
98// CHECK: call void [[CAP_FN2:@.+]](i32* [[GTID_ADDR]],
David Blaikieea3e51d2015-06-29 17:29:50 +000099// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +0000100// CHECK: br i1 %{{.+}}, label %[[OMP_THEN:.+]], label %[[OMP_ELSE:.+]]
101// CHECK: [[OMP_THEN]]
Alexey Bataev2377fe92015-09-10 08:12:02 +0000102// CHECK: call {{.*}}void {{.+}} @__kmpc_fork_call(%{{.+}}* @{{.+}}, i{{.+}} 0, void {{.+}}* [[CAP_FN3:@.+]] to void
Alexey Bataevd74d0602014-10-13 06:02:40 +0000103// CHECK: br label %[[OMP_END:.+]]
104// CHECK: [[OMP_ELSE]]
David Blaikieea3e51d2015-06-29 17:29:50 +0000105// CHECK: call {{.*}}void @__kmpc_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +0000106// CHECK: store i32 [[GTID]], i32* [[GTID_ADDR:%.+]],
107// CHECK: call void [[CAP_FN3]](i32* [[GTID_ADDR]],
David Blaikieea3e51d2015-06-29 17:29:50 +0000108// CHECK: call {{.*}}void @__kmpc_end_serialized_parallel(%{{.+}}* @{{.+}}, i32 [[GTID]])
Alexey Bataevd74d0602014-10-13 06:02:40 +0000109// CHECK: br label %[[OMP_END]]
110// CHECK: [[OMP_END]]
111
David Blaikieea3e51d2015-06-29 17:29:50 +0000112// CHECK: define internal {{.*}}void [[CAP_FN1]]
113// CHECK: call {{.*}}void @{{.+}}fn1
Alexey Bataevd74d0602014-10-13 06:02:40 +0000114// CHECK: ret void
115
David Blaikieea3e51d2015-06-29 17:29:50 +0000116// CHECK: define internal {{.*}}void [[CAP_FN2]]
117// CHECK: call {{.*}}void @{{.+}}fn2
Alexey Bataevd74d0602014-10-13 06:02:40 +0000118// CHECK: ret void
119
David Blaikieea3e51d2015-06-29 17:29:50 +0000120// CHECK: define internal {{.*}}void [[CAP_FN3]]
121// CHECK: call {{.*}}void @{{.+}}fn3
Alexey Bataevd74d0602014-10-13 06:02:40 +0000122// CHECK: ret void
123
124#endif