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
|
/* { dg-do run } */
/* { dg-require-effective-target avx } */
/* { dg-options "-O2 -mavx" } */
#include "avx-check.h"
#define CONTROL 0xCC
void static
avx_test (void)
{
union256 u, s1, s2;
float e [8];
s1.x = _mm256_set_ps (1, 2, 3, 4, 5, 6, 7, 8);
s2.x = _mm256_set_ps (9, 10, 11, 12, 13, 14, 15, 16);
u.x = _mm256_permute2f128_ps (s1.x, s2.x, CONTROL);
switch (CONTROL & 0x3)
{
case 0:
__builtin_memcpy (e, s1.a, 16);
break;
case 1:
__builtin_memcpy (e, s1.a+4, 16);
break;
case 2:
__builtin_memcpy (e, s2.a, 16);
break;
case 3:
__builtin_memcpy (e, s2.a+4, 16);
break;
default:
abort ();
}
switch ((CONTROL & 0xc)>>2)
{
case 0:
__builtin_memcpy (e+4, s1.a, 16);
break;
case 1:
__builtin_memcpy (e+4, s1.a+4, 16);
break;
case 2:
__builtin_memcpy (e+4, s2.a, 16);
break;
case 3:
__builtin_memcpy (e+4, s2.a+4, 16);
break;
default:
abort ();
}
if (CONTROL & (1<<3))
__builtin_memset (e, 0, 16);
if (CONTROL & (1<<7))
__builtin_memset (e+4, 0, 16);
if (check_union256 (u, e))
abort ();
}
|
