1/* { dg-do compile } */
2/* { dg-options "-mavx512bw -mavx512vl -O2" } */
3/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)"  1 } } */
4/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
5/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
6/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)"  1 } } */
7/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
8/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
9/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)"  1 } } */
10/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
11/* { dg-final { scan-assembler-times "vpermw\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
12
13#include <immintrin.h>
14
15volatile __m512i x1;
16volatile __m256i x2;
17volatile __m128i x3;
18volatile __mmask32 m1;
19volatile __mmask16 m2;
20volatile __mmask8 m3;
21
22void extern
23avx512bw_test (void)
24{
25  x1 = _mm512_permutexvar_epi16 (x1, x1);
26  x1 = _mm512_maskz_permutexvar_epi16 (m1, x1, x1);
27  x1 = _mm512_mask_permutexvar_epi16 (x1, m1, x1, x1);
28  x2 = _mm256_permutexvar_epi16 (x2, x2);
29  x2 = _mm256_maskz_permutexvar_epi16 (m2, x2, x2);
30  x2 = _mm256_mask_permutexvar_epi16 (x2, m2, x2, x2);
31  x3 = _mm_permutexvar_epi16 (x3, x3);
32  x3 = _mm_maskz_permutexvar_epi16 (m3, x3, x3);
33  x3 = _mm_mask_permutexvar_epi16 (x3, m3, x3, x3);
34}
35