aboutsummaryrefslogtreecommitdiff
path: root/libgomp/testsuite/libgomp.c-target/aarch64/private.c
blob: fed5370c8d04a2cd5820e18318105ea3cad898ff (plain)
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
/* { dg-do run { target aarch64_sve256_hw } } */
/* { dg-options "-msve-vector-bits=256 -fopenmp -O2" } */

#pragma GCC target "+sve"

#include <arm_sve.h>
#include <omp.h>

static void __attribute__ ((noipa))
compare_vec (svint32_t *x, svint32_t y)
{
  svbool_t p = svnot_b_z (svptrue_b32 (), svcmpeq_s32 (svptrue_b32 (), *x, y));

  if (svptest_any (svptrue_b32 (), p))
    __builtin_abort ();
}

void __attribute__ ((noipa))
private ()
{
  svint32_t a;
#pragma omp parallel private (a) num_threads (10)
  {
    a = svindex_s32 (omp_get_thread_num (), 0);

#pragma omp barrier
    compare_vec (&a, svindex_s32 (omp_get_thread_num (), 0));
  }
}

void __attribute__ ((noipa))
firstprivate ()
{
  svint32_t a = svindex_s32 (1,1);
  svint32_t b;

#pragma omp parallel private (b) firstprivate (a) num_threads (12)
  {
    compare_vec (&a, svindex_s32 (1, 1));
    b = svindex_s32 (omp_get_thread_num (), 0);

#pragma omp barrier
    compare_vec (&a, svindex_s32 (1, 1));
    compare_vec (&b, svindex_s32 (omp_get_thread_num (), 0));
    if (omp_get_thread_num () == 5)
      {
	a = svindex_s32 (1, 2);
	b = svindex_s32 (10, 0);
      }

#pragma omp barrier
    if (omp_get_thread_num () == 5)
      {
	compare_vec (&a, svindex_s32 (1, 2));
	compare_vec (&b, svindex_s32 (10, 0));
      }
    else
      {
	compare_vec (&a, svindex_s32 (1, 1));
	compare_vec (&b, svindex_s32 (omp_get_thread_num (), 0));
      }
  }
}

void __attribute__ ((noipa))
lastprivate ()
{
  svint32_t a = svindex_s32 (1,1);
  svint32_t b;
  int i;

#pragma omp parallel for private (a) lastprivate (b)
  for (i = 0; i < 16; i++)
    {
      b = svindex_s32 (i, 0);

      compare_vec (&b, svindex_s32 (i, 0));
      if (i == 5)
	{
	  a = svindex_s32 (1, 2);
	  b = svindex_s32 (10, 0);
	}
      else
	a = svindex_s32 (1, 1);

      if (i == 5)
	{
	  compare_vec (&a, svindex_s32 (1, 2));
	  compare_vec (&b, svindex_s32 (10, 0));
	}
      else
	{
	  compare_vec (&a, svindex_s32 (1, 1));
	  compare_vec (&b, svindex_s32 (i, 0));
	}
    }

  compare_vec (&b, svindex_s32 (15, 0));
}

int
main ()
{
  private ();
  firstprivate ();
  lastprivate ();
}