/* { dg-do run } */
/* { dg-require-effective-target avx2 } */
/* { dg-options "-O2 -mavx2" } */

#include <string.h>
#include "ssse3-vals.h"
#include "avx2-check.h"

/* Test the 256-bit form */
static void
avx2_test_palignr256 (__m256i t1, __m256i t2, unsigned int imm, __m256i * r)
{
  switch (imm)
    {
    case 0:
      *r = _mm256_alignr_epi8 (t1, t2, 0);
      break;
    case 1:
      *r = _mm256_alignr_epi8 (t1, t2, 1);
      break;
    case 2:
      *r = _mm256_alignr_epi8 (t1, t2, 2);
      break;
    case 3:
      *r = _mm256_alignr_epi8 (t1, t2, 3);
      break;
    case 4:
      *r = _mm256_alignr_epi8 (t1, t2, 4);
      break;
    case 5:
      *r = _mm256_alignr_epi8 (t1, t2, 5);
      break;
    case 6:
      *r = _mm256_alignr_epi8 (t1, t2, 6);
      break;
    case 7:
      *r = _mm256_alignr_epi8 (t1, t2, 7);
      break;
    case 8:
      *r = _mm256_alignr_epi8 (t1, t2, 8);
      break;
    case 9:
      *r = _mm256_alignr_epi8 (t1, t2, 9);
      break;
    case 10:
      *r = _mm256_alignr_epi8 (t1, t2, 10);
      break;
    case 11:
      *r = _mm256_alignr_epi8 (t1, t2, 11);
      break;
    case 12:
      *r = _mm256_alignr_epi8 (t1, t2, 12);
      break;
    case 13:
      *r = _mm256_alignr_epi8 (t1, t2, 13);
      break;
    case 14:
      *r = _mm256_alignr_epi8 (t1, t2, 14);
      break;
    case 15:
      *r = _mm256_alignr_epi8 (t1, t2, 15);
      break;
    case 16:
      *r = _mm256_alignr_epi8 (t1, t2, 16);
      break;
    case 17:
      *r = _mm256_alignr_epi8 (t1, t2, 17);
      break;
    case 18:
      *r = _mm256_alignr_epi8 (t1, t2, 18);
      break;
    case 19:
      *r = _mm256_alignr_epi8 (t1, t2, 19);
      break;
    case 20:
      *r = _mm256_alignr_epi8 (t1, t2, 20);
      break;
    case 21:
      *r = _mm256_alignr_epi8 (t1, t2, 21);
      break;
    case 22:
      *r = _mm256_alignr_epi8 (t1, t2, 22);
      break;
    case 23:
      *r = _mm256_alignr_epi8 (t1, t2, 23);
      break;
    case 24:
      *r = _mm256_alignr_epi8 (t1, t2, 24);
      break;
    case 25:
      *r = _mm256_alignr_epi8 (t1, t2, 25);
      break;
    case 26:
      *r = _mm256_alignr_epi8 (t1, t2, 26);
      break;
    case 27:
      *r = _mm256_alignr_epi8 (t1, t2, 27);
      break;
    case 28:
      *r = _mm256_alignr_epi8 (t1, t2, 28);
      break;
    case 29:
      *r = _mm256_alignr_epi8 (t1, t2, 29);
      break;
    case 30:
      *r = _mm256_alignr_epi8 (t1, t2, 30);
      break;
    case 31:
      *r = _mm256_alignr_epi8 (t1, t2, 31);
      break;
    default:
      *r = _mm256_alignr_epi8 (t1, t2, 32);
      break;
    }
}

/* Routine to manually compute the results */
static void
compute_correct_result_256 (int *i1, int *i2, unsigned int imm, int *r)
{
  char buf[32];
  char *bout = (char *) r;
  int i;

  /* Fill lowers 128 bit of ymm */
  memcpy (&buf[0], i2, 16);
  memcpy (&buf[16], i1, 16);

  for (i = 0; i < 16; i++)
    if (imm >= 32 || imm + i >= 32)
      bout[i] = 0;
    else
      bout[i] = buf[imm + i];

  /* Fill higher 128 bit of ymm */
  bout += 16;
  memcpy (&buf[0], i2 + 4, 16);
  memcpy (&buf[16], i1 + 4, 16);

  for (i = 0; i < 16; i++)
    if (imm >= 32 || imm + i >= 32)
      bout[i] = 0;
    else
      bout[i] = buf[imm + i];
}

static void
avx2_test (void)
{
  int i;
  int ck[8];
  int r[8];
  unsigned int imm;
  int fail = 0;

  union256i_q s1, s2, d;

  for (i = 0; i < 256; i += 16)
    for (imm = 0; imm < 100; imm++)
      {
	/* Recompute the results for 256-bits */
	compute_correct_result_256 (&vals[i + 0], &vals[i + 8], imm, ck);

	s1.x = _mm256_loadu_si256 ((__m256i *) & vals[i + 0]);
	s2.x = _mm256_loadu_si256 ((__m256i *) & vals[i + 8]);

	/* Run the 256-bit tests */
	avx2_test_palignr256 (s1.x, s2.x, imm, &d.x);

	_mm256_storeu_si256 ((__m256i *) r, d.x);

	fail += checkVi (r, ck, 8);
      }

  if (fail != 0)
    abort ();
}