gcc/testsuite/gcc.target/i386/avx512bw-vmovdqu8-1.c

   1 /* { dg-do compile } */
   2 /* { dg-options "-mavx512bw -mavx512vl -O2" } */
   3 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
   4 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
   5 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
   6 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
   7 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
   8 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
   9 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*\\)\[^\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
  10 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*\\)\[^\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
  11 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*\\)\[^\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
  12 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*\\)\[^\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
  13 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*\\)\[^\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
  14 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*\\)\[^\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */
  15 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\]*\\)\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
  16 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\]*\\)\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
  17 /* { dg-final { scan-assembler-times "vmovdqu8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\]*\\)\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
  18
  19 #include <immintrin.h>
  20
  21 char *p;
  22 volatile __m512i x1, yy;
  23 volatile __m256i x2, y2;
  24 volatile __m128i x3, y3;
  25 volatile __mmask64 m64;
  26 volatile __mmask32 m32;
  27 volatile __mmask16 m16;
  28
  29 void extern
  30 avx512bw_test (void)
  31 {
  32   x1 = _mm512_mask_mov_epi8 (x1, m64, yy);
  33   x2 = _mm256_mask_mov_epi8 (x2, m32, y2);
  34   x3 = _mm_mask_mov_epi8 (x3, m16, y3);
  35
  36   x1 = _mm512_maskz_mov_epi8 (m64, yy);
  37   x2 = _mm256_maskz_mov_epi8 (m32, y2);
  38   x3 = _mm_maskz_mov_epi8 (m16, y3);
  39
  40   x1 = _mm512_mask_loadu_epi8 (x1, m64, p);
  41   x2 = _mm256_mask_loadu_epi8 (x2, m32, p);
  42   x3 = _mm_mask_loadu_epi8 (x3, m16, p);
  43
  44   x1 = _mm512_maskz_loadu_epi8 (m64, p);
  45   x2 = _mm256_maskz_loadu_epi8 (m32, p);
  46   x3 = _mm_maskz_loadu_epi8 (m16, p);
  47
  48   _mm512_mask_storeu_epi8 (p, m64, x1);
  49   _mm256_mask_storeu_epi8 (p, m32, x2);
  50   _mm_mask_storeu_epi8 (p, m16, x3);
  51 }