1/* { dg-do run } */
2/* { dg-require-effective-target avx512er } */
3/* { dg-options "-O2 -mavx512er" } */
4
5#include "avx512er-check.h"
6#include "avx512f-mask-type.h"
7#include "avx512f-helper.h"
8
9void static
10compute_vrcp28ps (float *s, float *r)
11{
12  int i;
13  for (i = 0; i < 16; i++)
14    r[i] = 1.0 / s[i];
15}
16
17void static
18avx512er_test (void)
19{
20  union512 src, res1, res2, res3;
21  __mmask16 mask = MASK_VALUE;
22  float res_ref[16];
23  int i;
24
25  for (i = 0; i < 16; i++)
26    {
27      src.a[i] = 179.345 - 6.5645 * i;
28      res2.a[i] = DEFAULT_VALUE;
29    }
30
31  res1.x = _mm512_rcp28_ps (src.x);
32  res2.x = _mm512_mask_rcp28_ps (res2.x, mask, src.x);
33  res3.x = _mm512_maskz_rcp28_ps (mask, src.x);
34
35  compute_vrcp28ps (src.a, res_ref);
36
37  if (check_rough_union512 (res1, res_ref, 0.0001))
38    abort ();
39
40  MASK_MERGE ()(res_ref, mask, 16);
41  if (check_rough_union512 (res2, res_ref, 0.0001))
42    abort ();
43
44  MASK_ZERO ()(res_ref, mask, 16);
45  if (check_rough_union512 (res3, res_ref, 0.0001))
46    abort ();
47}
48