summaryrefslogtreecommitdiff
path: root/gcc/testsuite/gcc.target/i386/avx-vperm2f128-256-1.c
blob: 99abca189b17b86768a9381633809f4c0bb7dbf1 (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
/* { 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 ();
}