1 | // RUN: %libomp-compile && env OMP_MAX_TASK_PRIORITY='2' %libomp-run |
2 | |
3 | // Test OMP 4.5 task priorities |
4 | // Higher priority task supposed to be executed before lower priority task. |
5 | |
6 | #include <stdio.h> |
7 | #include <omp.h> |
8 | |
9 | #include "omp_my_sleep.h" |
10 | // delay(n) - sleep n ms |
11 | #define delay(n) my_sleep(((double)n)/1000.0) |
12 | |
13 | int main ( void ) { |
14 | int passed; |
15 | passed = (omp_get_max_task_priority() == 2); |
16 | printf(format: "Got %d max priority via env\n" , omp_get_max_task_priority()); |
17 | if(!passed) { |
18 | printf( format: "failed\n" ); |
19 | return 1; |
20 | } |
21 | printf(format: "parallel 1 spawns 4 tasks for primary thread to execute\n" ); |
22 | #pragma omp parallel num_threads(2) |
23 | { |
24 | int th = omp_get_thread_num(); |
25 | if (th == 0) // primary thread |
26 | { |
27 | #pragma omp task priority(1) |
28 | { // middle priority |
29 | int val, t = omp_get_thread_num(); |
30 | #pragma omp atomic capture |
31 | val = passed++; |
32 | printf(format: "P1: val = %d, thread gen %d, thread exe %d\n" , val, th, t); |
33 | delay(10); // sleep 10 ms |
34 | } |
35 | #pragma omp task priority(2) |
36 | { // high priority |
37 | int val, t = omp_get_thread_num(); |
38 | #pragma omp atomic capture |
39 | val = passed++; |
40 | printf(format: "P2: val = %d, thread gen %d, thread exe %d\n" , val, th, t); |
41 | delay(20); // sleep 20 ms |
42 | } |
43 | #pragma omp task priority(0) |
44 | { // low priority specified explicitly |
45 | int val, t = omp_get_thread_num(); |
46 | #pragma omp atomic capture |
47 | val = passed++; |
48 | printf(format: "P0exp: val = %d, thread gen %d, thread exe %d\n" , val, th, t); |
49 | delay(1); // sleep 1 ms |
50 | } |
51 | #pragma omp task |
52 | { // low priority by default |
53 | int val, t = omp_get_thread_num(); |
54 | #pragma omp atomic capture |
55 | val = passed++; |
56 | printf(format: "P0imp: val = %d, thread gen %d, thread exe %d\n" , val, th, t); |
57 | delay(1); // sleep 1 ms |
58 | } |
59 | } else { |
60 | // wait for the primary thread to finish all tasks |
61 | int wait = 0; |
62 | do { |
63 | delay(5); |
64 | #pragma omp atomic read |
65 | wait = passed; |
66 | } while (wait < 5); |
67 | } |
68 | } |
69 | printf(format: "parallel 2 spawns 4 tasks for worker thread to execute\n" ); |
70 | #pragma omp parallel num_threads(2) |
71 | { |
72 | int th = omp_get_thread_num(); |
73 | if (th == 0) // primary thread |
74 | { |
75 | #pragma omp task priority(1) |
76 | { // middle priority |
77 | int val, t = omp_get_thread_num(); |
78 | #pragma omp atomic capture |
79 | val = passed++; |
80 | printf(format: "P1: val = %d, thread gen %d, thread exe %d\n" , val, th, t); |
81 | delay(10); // sleep 10 ms |
82 | } |
83 | #pragma omp task priority(2) |
84 | { // high priority |
85 | int val, t = omp_get_thread_num(); |
86 | #pragma omp atomic capture |
87 | val = passed++; |
88 | printf(format: "P2: val = %d, thread gen %d, thread exe %d\n" , val, th, t); |
89 | delay(20); // sleep 20 ms |
90 | } |
91 | #pragma omp task priority(0) |
92 | { // low priority specified explicitly |
93 | int val, t = omp_get_thread_num(); |
94 | #pragma omp atomic capture |
95 | val = passed++; |
96 | printf(format: "P0exp: val = %d, thread gen %d, thread exe %d\n" , val, th, t); |
97 | delay(1); // sleep 1 ms |
98 | } |
99 | #pragma omp task |
100 | { // low priority by default |
101 | int val, t = omp_get_thread_num(); |
102 | #pragma omp atomic capture |
103 | val = passed++; |
104 | printf(format: "P0imp: val = %d, thread gen %d, thread exe %d\n" , val, th, t); |
105 | delay(1); // sleep 1 ms |
106 | } |
107 | // signal creation of all tasks: passed = 5 + 1 = 6 |
108 | #pragma omp atomic |
109 | passed++; |
110 | // wait for completion of all 4 tasks |
111 | int wait = 0; |
112 | do { |
113 | delay(5); |
114 | #pragma omp atomic read |
115 | wait = passed; |
116 | } while (wait < 10); // passed = 6 + 4 = 10 |
117 | } else { |
118 | // wait for the primary thread to create all tasks |
119 | int wait = 0; |
120 | do { |
121 | delay(5); |
122 | #pragma omp atomic read |
123 | wait = passed; |
124 | } while (wait < 6); |
125 | // go execute 4 tasks created by primary thread |
126 | } |
127 | } |
128 | if (passed != 10) { |
129 | printf(format: "failed, passed = %d (should be 10)\n" , passed); |
130 | return 1; |
131 | } |
132 | printf(format: "passed\n" ); |
133 | return 0; |
134 | } |
135 | // CHECK: parallel 1 |
136 | // CHECK-NEXT: P2 |
137 | // CHECK-NEXT: P1 |
138 | // CHECK-NEXT: P0 |
139 | // CHECK-NEXT: P0 |
140 | // CHECK-NEXT: parallel 2 |
141 | // CHECK-NEXT: P2 |
142 | // CHECK-NEXT: P1 |
143 | // CHECK-NEXT: P0 |
144 | // CHECK-NEXT: P0 |
145 | // CHECK: passed |
146 | |