/* { dg-do run } */
/* { dg-require-effective-target avx512f } */
/* { dg-options "-O2 -mavx512f" } */

#include <string.h>
#include "avx512f-check.h"
#include "avx512f-helper.h"

void static
avx512f_test (void)
{
  union512i_q s1;
  union256i_q res1, res2, res3;
  __mmask8 mask = 0xBA;
  long long int res_ref[4];
  int j;

  for (j = 0; j < 8; j++)
    s1.a[j] = j * j;

  for (j = 0; j < 4; j++)
    {
      res1.a[j] = DEFAULT_VALUE;
      res2.a[j] = DEFAULT_VALUE;
      res3.a[j] = DEFAULT_VALUE;
    }
  res1.x = _mm512_extracti64x4_epi64 (s1.x, 0);
  res2.x = _mm512_mask_extracti64x4_epi64 (res2.x, mask, s1.x, 0);
  res3.x = _mm512_maskz_extracti64x4_epi64 (mask, s1.x, 0);

  memset (res_ref, 0, 32);
  memcpy (res_ref, s1.a, 32);

  if (check_union256i_q (res1, res_ref))
    abort ();

  MASK_MERGE (i_q) (res_ref, mask, 4);
  if (check_union256i_q (res2, res_ref))
    abort ();

  MASK_ZERO (i_q) (res_ref, mask, 4);
  if (check_union256i_q (res3, res_ref))
    abort ();

  res1.x = _mm512_extracti64x4_epi64 (s1.x, 1);
  res2.x = _mm512_mask_extracti64x4_epi64 (res2.x, mask, s1.x, 1);
  res3.x = _mm512_maskz_extracti64x4_epi64 (mask, s1.x, 1);

  memset (res_ref, 0, 32);
  memcpy (res_ref, s1.a + 4, 32);

  if (check_union256i_q (res1, res_ref))
    abort ();

  MASK_MERGE (i_q) (res_ref, mask, 4);
  if (check_union256i_q (res2, res_ref))
    abort ();

  MASK_ZERO (i_q) (res_ref, mask, 4);
  if (check_union256i_q (res3, res_ref))
    abort ();
}