blob: 289f058966448fbf6590ee182c8eac91b6b2e7cc [file] [log] [blame]
Reid Kleckner06f19a02018-01-02 21:34:16 +00001// RUN: %clang_cc1 -verify -fopenmp -x c++ -triple x86_64-pc-windows-msvc18.0.0 -std=c++11 -fms-compatibility-version=18 -fms-extensions -emit-llvm %s -fexceptions -fcxx-exceptions -o - | FileCheck %s
Alexey Bataeva8a9153a2017-12-29 18:07:07 +00002
Reid Kleckner06f19a02018-01-02 21:34:16 +00003// RUN: %clang_cc1 -verify -fopenmp-simd -x c++ -triple x86_64-pc-windows-msvc18.0.0 -std=c++11 -fms-compatibility-version=18 -fms-extensions -emit-llvm %s -fexceptions -fcxx-exceptions -o - | FileCheck --check-prefix SIMD-ONLY0 %s
4
Alexey Bataeva8a9153a2017-12-29 18:07:07 +00005// SIMD-ONLY0-NOT: {{__kmpc|__tgt}}
Alexey Bataev0e1b4582017-11-02 14:25:34 +00006// expected-no-diagnostics
7
8void foo();
9void bar();
10
Alexey Bataev5d2c9a42017-11-02 18:55:05 +000011struct Test {
12 static void main() {
13 int failed = 0;
14 int j = 2;
15
16#pragma omp parallel
17 {
18 int local_j = 3;
19#pragma omp single copyprivate(local_j)
20 {
21 local_j = 4;
22 }
23
24 // Assure reports a data race, but value written to "j"
25 // should always be the same.
26 j = local_j;
27 }
28
29 }
30};
31
Alexey Bataev0e1b4582017-11-02 14:25:34 +000032// CHECK-LABEL: @main
33int main() {
Alexey Bataev5d2c9a42017-11-02 18:55:05 +000034 // CHECK: call void @{{.+}}main
35 Test::main();
Alexey Bataeva4fa0b82018-04-16 17:59:34 +000036 // CHECK: call void (%struct.ident_t*, i32, void (i32*, i32*, ...)*, ...) @__kmpc_fork_call(%struct.ident_t* {{.*}}@0, i32 0, void (i32*, i32*, ...)* bitcast (void (i32*, i32*)* [[OUTLINED:@.+]] to void (i32*, i32*, ...)*))
Alexey Bataev0e1b4582017-11-02 14:25:34 +000037#pragma omp parallel
38 {
39 try {
40 foo();
41 } catch (int t) {
42#pragma omp critical
43 {
44 bar();
45 };
46 }
47 };
48 // CHECK: ret i32 0
49 return 0;
50}
51
52// CHECK: define internal void [[OUTLINED]](
Alexey Bataeva4fa0b82018-04-16 17:59:34 +000053// CHECK: [[GID:%.+]] = {{.*}}call i32 @__kmpc_global_thread_num(%struct.ident_t* {{.*}}@0)
Alexey Bataev0e1b4582017-11-02 14:25:34 +000054// CHECK: invoke void @{{.+}}foo
Reid Kleckner06f19a02018-01-02 21:34:16 +000055// CHECK: [[CATCHSWITCH:%.+]] = catchswitch within none
56// CHECK: [[CATCHPAD:%.+]] = catchpad within [[CATCHSWITCH]]
Alexey Bataeva4fa0b82018-04-16 17:59:34 +000057// CHECK: call void @__kmpc_critical(%struct.ident_t* {{.*}}@0, i32 [[GID]],
Alexey Bataev0e1b4582017-11-02 14:25:34 +000058// CHECK: invoke void @{{.+}}bar
Alexey Bataeva4fa0b82018-04-16 17:59:34 +000059// CHECK: call void @__kmpc_end_critical(%struct.ident_t* {{.*}}@0, i32 [[GID]],
Reid Kleckner06f19a02018-01-02 21:34:16 +000060// CHECK: catchret from [[CATCHPAD]] to
61// CHECK: cleanuppad within [[CATCHPAD]] []
Alexey Bataeva4fa0b82018-04-16 17:59:34 +000062// CHECK-NEXT: call void @__kmpc_end_critical(%struct.ident_t* {{.*}}@0, i32 [[GID]],
Reid Kleckner06f19a02018-01-02 21:34:16 +000063// CHECK-NEXT: cleanupret from {{.*}} unwind label %[[CATCHTERM:[^ ]+]]
64// CHECK: cleanuppad within none []
Reid Klecknerfb931542018-03-16 20:36:49 +000065// CHECK-NEXT: call void @"?terminate@@YAXXZ"() #5 [ "funclet"(token %{{.*}}) ]
Reid Kleckner06f19a02018-01-02 21:34:16 +000066// CHECK-NEXT: unreachable
67// CHECK: [[CATCHTERM]]
68// CHECK-NEXT: cleanuppad within [[CATCHPAD]] []
Reid Klecknerfb931542018-03-16 20:36:49 +000069// CHECK-NEXT: call void @"?terminate@@YAXXZ"() #5 [ "funclet"(token %{{.*}}) ]
Reid Kleckner06f19a02018-01-02 21:34:16 +000070// CHECK-NEXT: unreachable