xref: /llvm-project/openmp/runtime/test/tasking/kmp_taskwait_depend_in.c (revision 8e29b4b323b87f3855dc71abf1e3f3d48952a4e4)
1*8e29b4b3SAndreyChurbanov // RUN: %libomp-compile-and-run
2*8e29b4b3SAndreyChurbanov 
3*8e29b4b3SAndreyChurbanov // test checks IN dep kind in depend clause on taskwait construct
4*8e29b4b3SAndreyChurbanov // uses codegen emulation
5*8e29b4b3SAndreyChurbanov #include <stdio.h>
6*8e29b4b3SAndreyChurbanov #include <omp.h>
7*8e29b4b3SAndreyChurbanov // ---------------------------------------------------------------------------
8*8e29b4b3SAndreyChurbanov // internal data to emulate compiler codegen
9*8e29b4b3SAndreyChurbanov typedef struct DEP {
10*8e29b4b3SAndreyChurbanov   size_t addr;
11*8e29b4b3SAndreyChurbanov   size_t len;
12*8e29b4b3SAndreyChurbanov   unsigned char flags;
13*8e29b4b3SAndreyChurbanov } _dep;
14*8e29b4b3SAndreyChurbanov typedef struct ID {
15*8e29b4b3SAndreyChurbanov   int reserved_1;
16*8e29b4b3SAndreyChurbanov   int flags;
17*8e29b4b3SAndreyChurbanov   int reserved_2;
18*8e29b4b3SAndreyChurbanov   int reserved_3;
19*8e29b4b3SAndreyChurbanov   char *psource;
20*8e29b4b3SAndreyChurbanov } _id;
21*8e29b4b3SAndreyChurbanov 
22*8e29b4b3SAndreyChurbanov #ifdef __cplusplus
23*8e29b4b3SAndreyChurbanov extern "C" {
24*8e29b4b3SAndreyChurbanov #endif
25*8e29b4b3SAndreyChurbanov extern int __kmpc_global_thread_num(_id*);
26*8e29b4b3SAndreyChurbanov extern void __kmpc_omp_wait_deps(_id *, int, int, _dep *, int, _dep *);
27*8e29b4b3SAndreyChurbanov #ifdef __cplusplus
28*8e29b4b3SAndreyChurbanov } // extern "C"
29*8e29b4b3SAndreyChurbanov #endif
30*8e29b4b3SAndreyChurbanov 
main()31*8e29b4b3SAndreyChurbanov int main()
32*8e29b4b3SAndreyChurbanov {
33*8e29b4b3SAndreyChurbanov   int i1,i2,i3;
34*8e29b4b3SAndreyChurbanov   omp_set_num_threads(2);
35*8e29b4b3SAndreyChurbanov   printf("addresses: %p %p %p\n", &i1, &i2, &i3);
36*8e29b4b3SAndreyChurbanov   #pragma omp parallel
37*8e29b4b3SAndreyChurbanov   {
38*8e29b4b3SAndreyChurbanov     int t = omp_get_thread_num();
39*8e29b4b3SAndreyChurbanov     printf("thread %d enters parallel\n", t);
40*8e29b4b3SAndreyChurbanov     #pragma omp single
41*8e29b4b3SAndreyChurbanov     {
42*8e29b4b3SAndreyChurbanov       #pragma omp task depend(in: i3)
43*8e29b4b3SAndreyChurbanov       {
44*8e29b4b3SAndreyChurbanov         int th = omp_get_thread_num();
45*8e29b4b3SAndreyChurbanov         printf("task 0 created by th %d, executed by th %d\n", t, th);
46*8e29b4b3SAndreyChurbanov       }
47*8e29b4b3SAndreyChurbanov       #pragma omp task depend(in: i2)
48*8e29b4b3SAndreyChurbanov       {
49*8e29b4b3SAndreyChurbanov         int th = omp_get_thread_num();
50*8e29b4b3SAndreyChurbanov         printf("task 1 created by th %d, executed by th %d\n", t, th);
51*8e29b4b3SAndreyChurbanov       }
52*8e29b4b3SAndreyChurbanov //      #pragma omp taskwait depend(in: i1, i2)
53*8e29b4b3SAndreyChurbanov       {
54*8e29b4b3SAndreyChurbanov         _dep sdep[2];
55*8e29b4b3SAndreyChurbanov         static _id loc = {0, 2, 0, 0, ";test9.c;func;60;0;;"};
56*8e29b4b3SAndreyChurbanov         int gtid = __kmpc_global_thread_num(&loc);
57*8e29b4b3SAndreyChurbanov         sdep[0].addr = (size_t)&i2;
58*8e29b4b3SAndreyChurbanov         sdep[0].flags = 1; // 1-in, 2-out, 3-inout, 4-mtx, 8-inoutset
59*8e29b4b3SAndreyChurbanov         sdep[1].addr = (size_t)&i1;
60*8e29b4b3SAndreyChurbanov         sdep[1].flags = 1; // in
61*8e29b4b3SAndreyChurbanov         __kmpc_omp_wait_deps(&loc, gtid, 2, sdep, 0, NULL);
62*8e29b4b3SAndreyChurbanov       }
63*8e29b4b3SAndreyChurbanov       printf("single done\n");
64*8e29b4b3SAndreyChurbanov     }
65*8e29b4b3SAndreyChurbanov   }
66*8e29b4b3SAndreyChurbanov   printf("passed\n");
67*8e29b4b3SAndreyChurbanov   return 0;
68*8e29b4b3SAndreyChurbanov }
69