/* { dg-do compile} */
/* { dg-options "-O2 -mavx512fp16 -mavx512vl" } */

#include <immintrin.h>
void
__attribute__ ((noinline, noclone))
store512_ph (void *p, __m512h a)
{
  _mm512_store_ph (p, a);
}

/* { dg-final { scan-assembler-times "vmovdqa64\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\]*\\)" 1 } } */

void
__attribute__ ((noinline, noclone))
store256_ph (void *p, __m256h a)
{
  _mm256_store_ph (p, a);
}

/* { dg-final { scan-assembler-times "vmovdqa64\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\]*\\)" 1 } } */

void
__attribute__ ((noinline, noclone))
store_ph (void *p, __m128h a)
{
  _mm_store_ph (p, a);
}

/* { dg-final { scan-assembler-times "vmovdqa64\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\]*\\)" 1 } } */

__m512h
__attribute__ ((noinline, noclone))
load512_ph (void const *p)
{
  return _mm512_load_ph (p);
}

/* { dg-final { scan-assembler-times "vmovdqa64\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\]*\\)" 1 } } */

__m256h
__attribute__ ((noinline, noclone))
load256_ph (void const *p)
{
  return _mm256_load_ph (p);
}

/* { dg-final { scan-assembler-times "vmovdqa64\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\]*\\)" 1 } } */

__m128h
__attribute__ ((noinline, noclone))
load_ph (void const *p)
{
  return _mm_load_ph (p);
}
/* { dg-final { scan-assembler-times "vmovdqa64\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\]*\\)" 1 } } */

__m512h
__attribute__ ((noinline, noclone))
load512u_ph (void const *p)
{
  return _mm512_loadu_ph (p);
}

/* { dg-final { scan-assembler-times "vmovdqu16\[ \\t\]*\[^,\]*,\[^\{\n\]*%zmm\[0-9\]" 1 } } */

__m256h
__attribute__ ((noinline, noclone))
load256u_ph (void const *p)
{
  return _mm256_loadu_ph (p);
}

/* { dg-final { scan-assembler-times "vmovdqu16\[ \\t\]*\[^,\]*,\[^\{\n\]*%ymm\[0-9\]" 1 } } */

__m128h
__attribute__ ((noinline, noclone))
load128u_ph (void const *p)
{
  return _mm_loadu_ph (p);
}

/* { dg-final { scan-assembler-times "vmovdqu16\[ \\t\]*\[^,\]*,\[^\{\n\]*%xmm\[0-9\]" 1 } } */

void
__attribute__ ((noinline, noclone))
store512u_ph (void *p, __m512h a)
{
  return _mm512_storeu_ph (p, a);
}

/* { dg-final { scan-assembler-times "vmovdqu16\[ \\t\]*\[^\{\n\]*%zmm\[0-9\], *\[^,\]*" 1 } } */

void
__attribute__ ((noinline, noclone))
store256u_ph (void *p, __m256h a)
{
  return _mm256_storeu_ph (p, a);
}

/* { dg-final { scan-assembler-times "vmovdqu16\[ \\t\]*\[^\{\n\]*%ymm\[0-9\], *\[^,\]*" 1 } } */

void
__attribute__ ((noinline, noclone))
storeu_ph (void *p, __m128h a)
{
  return _mm_storeu_ph (p, a);
}

/* { dg-final { scan-assembler-times "vmovdqu16\[ \\t\]*\[^\{\n\]*%xmm\[0-9\], *\[^,\]*" 1 } } */

__m512h
__attribute__ ((noinline, noclone))
abs512_ph (__m512h a)
{
  return _mm512_abs_ph (a);
}

/* { dg-final { scan-assembler-times "vpbroadcastd\[^\n\]*%zmm\[0-9\]+" 1 { target { ! ia32 } } } } */
/* { dg-final { scan-assembler-times "vpandd\[^\n\]*%zmm\[0-9\]+" 1 } } */

__m256h
__attribute__ ((noinline, noclone))
abs256_ph (__m256h a)
{
  return _mm256_abs_ph (a);
}

/* { dg-final { scan-assembler-times "vpbroadcastq\[^\n\]*%ymm\[0-9\]+" 1 { target { ! ia32 } } } } */
/* { dg-final { scan-assembler-times "vpand\[^\n\]*%ymm\[0-9\]+" 1 } } */

__m128h
__attribute__ ((noinline, noclone))
abs_ph (__m128h a)
{
  return _mm_abs_ph (a);
}

/* { dg-final { scan-assembler-times "vpbroadcastq\[^\n\]*%xmm\[0-9\]+" 1 { target { ! ia32 } } } } */
/* { dg-final { scan-assembler-times "vpand\[^\n\]*%xmm\[0-9\]+" 1 } } */