1/* { dg-do compile } */
2/* { dg-options "-mavx512vl -O2" } */
3/* { dg-final { scan-assembler-times "vpexpandd\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)"  1 } } */
4/* { dg-final { scan-assembler-times "vpexpandd\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)"  1 } } */
5/* { dg-final { scan-assembler-times "vpexpandd\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)"  1 } } */
6/* { dg-final { scan-assembler-times "vpexpandd\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)"  1 } } */
7/* { dg-final { scan-assembler-times "vpexpandd\[ \\t\]+\[^\{\n\]*\\(\[^\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)"  1 } } */
8/* { dg-final { scan-assembler-times "vpexpandd\[ \\t\]+\[^\{\n\]*\\(\[^\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)"  1 } } */
9/* { dg-final { scan-assembler-times "vpexpandd\[ \\t\]+\[^\{\n\]*\\(\[^\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)"  1 } } */
10/* { dg-final { scan-assembler-times "vpexpandd\[ \\t\]+\[^\{\n\]*\\(\[^\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)"  1 } } */
11
12#include <immintrin.h>
13
14int *p;
15volatile __m256i x1;
16volatile __m128i x2;
17volatile __mmask8 m;
18
19void extern
20avx512vl_test (void)
21{
22  x1 = _mm256_mask_expand_epi32 (x1, m, x1);
23  x2 = _mm_mask_expand_epi32 (x2, m, x2);
24
25  x1 = _mm256_maskz_expand_epi32 (m, x1);
26  x2 = _mm_maskz_expand_epi32 (m, x2);
27
28  x1 = _mm256_mask_expandloadu_epi32 (x1, m, p);
29  x2 = _mm_mask_expandloadu_epi32 (x2, m, p);
30
31  x1 = _mm256_maskz_expandloadu_epi32 (m, p);
32  x2 = _mm_maskz_expandloadu_epi32 (m, p);
33}
34