clang/test/CodeGen/X86/avx512vbmi2-builtins.c

   1 // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vbmi2 -emit-llvm -o - -Wall -Werror | FileCheck %s
   2
   3 #include <immintrin.h>
   4
   5 __m512i test_mm512_mask_compress_epi16(__m512i __S, __mmask32 __U, __m512i __D) {
   6   // CHECK-LABEL: @test_mm512_mask_compress_epi16
   7   // CHECK: @llvm.x86.avx512.mask.compress
   8   return _mm512_mask_compress_epi16(__S, __U, __D);
   9 }
  10
  11 __m512i test_mm512_maskz_compress_epi16(__mmask32 __U, __m512i __D) {
  12   // CHECK-LABEL: @test_mm512_maskz_compress_epi16
  13   // CHECK: @llvm.x86.avx512.mask.compress
  14   return _mm512_maskz_compress_epi16(__U, __D);
  15 }
  16
  17 __m512i test_mm512_mask_compress_epi8(__m512i __S, __mmask64 __U, __m512i __D) {
  18   // CHECK-LABEL: @test_mm512_mask_compress_epi8
  19   // CHECK: @llvm.x86.avx512.mask.compress
  20   return _mm512_mask_compress_epi8(__S, __U, __D);
  21 }
  22
  23 __m512i test_mm512_maskz_compress_epi8(__mmask64 __U, __m512i __D) {
  24   // CHECK-LABEL: @test_mm512_maskz_compress_epi8
  25   // CHECK: @llvm.x86.avx512.mask.compress
  26   return _mm512_maskz_compress_epi8(__U, __D);
  27 }
  28
  29 void test_mm512_mask_compressstoreu_epi16(void *__P, __mmask32 __U, __m512i __D) {
  30   // CHECK-LABEL: @test_mm512_mask_compressstoreu_epi16
  31   // CHECK: @llvm.masked.compressstore.v32i16(<32 x i16> %{{.*}}, ptr %{{.*}}, <32 x i1> %{{.*}})
  32   _mm512_mask_compressstoreu_epi16(__P, __U, __D);
  33 }
  34
  35 void test_mm512_mask_compressstoreu_epi8(void *__P, __mmask64 __U, __m512i __D) {
  36   // CHECK-LABEL: @test_mm512_mask_compressstoreu_epi8
  37   // CHECK: @llvm.masked.compressstore.v64i8(<64 x i8> %{{.*}}, ptr %{{.*}}, <64 x i1> %{{.*}})
  38   _mm512_mask_compressstoreu_epi8(__P, __U, __D);
  39 }
  40
  41 __m512i test_mm512_mask_expand_epi16(__m512i __S, __mmask32 __U, __m512i __D) {
  42   // CHECK-LABEL: @test_mm512_mask_expand_epi16
  43   // CHECK: @llvm.x86.avx512.mask.expand
  44   return _mm512_mask_expand_epi16(__S, __U, __D);
  45 }
  46
  47 __m512i test_mm512_maskz_expand_epi16(__mmask32 __U, __m512i __D) {
  48   // CHECK-LABEL: @test_mm512_maskz_expand_epi16
  49   // CHECK: @llvm.x86.avx512.mask.expand
  50   return _mm512_maskz_expand_epi16(__U, __D);
  51 }
  52
  53 __m512i test_mm512_mask_expand_epi8(__m512i __S, __mmask64 __U, __m512i __D) {
  54   // CHECK-LABEL: @test_mm512_mask_expand_epi8
  55   // CHECK: @llvm.x86.avx512.mask.expand
  56   return _mm512_mask_expand_epi8(__S, __U, __D);
  57 }
  58
  59 __m512i test_mm512_maskz_expand_epi8(__mmask64 __U, __m512i __D) {
  60   // CHECK-LABEL: @test_mm512_maskz_expand_epi8
  61   // CHECK: @llvm.x86.avx512.mask.expand
  62   return _mm512_maskz_expand_epi8(__U, __D);
  63 }
  64
  65 __m512i test_mm512_mask_expandloadu_epi16(__m512i __S, __mmask32 __U, void const* __P) {
  66   // CHECK-LABEL: @test_mm512_mask_expandloadu_epi16
  67   // CHECK: @llvm.masked.expandload.v32i16(ptr %{{.*}}, <32 x i1> %{{.*}}, <32 x i16> %{{.*}})
  68   return _mm512_mask_expandloadu_epi16(__S, __U, __P);
  69 }
  70
  71 __m512i test_mm512_maskz_expandloadu_epi16(__mmask32 __U, void const* __P) {
  72   // CHECK-LABEL: @test_mm512_maskz_expandloadu_epi16
  73   // CHECK: @llvm.masked.expandload.v32i16(ptr %{{.*}}, <32 x i1> %{{.*}}, <32 x i16> %{{.*}})
  74   return _mm512_maskz_expandloadu_epi16(__U, __P);
  75 }
  76
  77 __m512i test_mm512_mask_expandloadu_epi8(__m512i __S, __mmask64 __U, void const* __P) {
  78   // CHECK-LABEL: @test_mm512_mask_expandloadu_epi8
  79   // CHECK: @llvm.masked.expandload.v64i8(ptr %{{.*}}, <64 x i1> %{{.*}}, <64 x i8> %{{.*}})
  80   return _mm512_mask_expandloadu_epi8(__S, __U, __P);
  81 }
  82
  83 __m512i test_mm512_maskz_expandloadu_epi8(__mmask64 __U, void const* __P) {
  84   // CHECK-LABEL: @test_mm512_maskz_expandloadu_epi8
  85   // CHECK: @llvm.masked.expandload.v64i8(ptr %{{.*}}, <64 x i1> %{{.*}}, <64 x i8> %{{.*}})
  86   return _mm512_maskz_expandloadu_epi8(__U, __P);
  87 }
  88
  89 __m512i test_mm512_mask_shldi_epi64(__m512i __S, __mmask8 __U, __m512i __A, __m512i __B) {
  90   // CHECK-LABEL: @test_mm512_mask_shldi_epi64
  91   // CHECK: @llvm.fshl.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> splat (i64 47))
  92   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
  93   return _mm512_mask_shldi_epi64(__S, __U, __A, __B, 47);
  94 }
  95
  96 __m512i test_mm512_maskz_shldi_epi64(__mmask8 __U, __m512i __A, __m512i __B) {
  97   // CHECK-LABEL: @test_mm512_maskz_shldi_epi64
  98   // CHECK: @llvm.fshl.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> splat (i64 63))
  99   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
 100   return _mm512_maskz_shldi_epi64(__U, __A, __B, 63);
 101 }
 102
 103 __m512i test_mm512_shldi_epi64(__m512i __A, __m512i __B) {
 104   // CHECK-LABEL: @test_mm512_shldi_epi64
 105   // CHECK: @llvm.fshl.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> splat (i64 31))
 106   return _mm512_shldi_epi64(__A, __B, 31);
 107 }
 108
 109 __m512i test_mm512_mask_shldi_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) {
 110   // CHECK-LABEL: @test_mm512_mask_shldi_epi32
 111   // CHECK: @llvm.fshl.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> splat (i32 7))
 112   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
 113   return _mm512_mask_shldi_epi32(__S, __U, __A, __B, 7);
 114 }
 115
 116 __m512i test_mm512_maskz_shldi_epi32(__mmask16 __U, __m512i __A, __m512i __B) {
 117   // CHECK-LABEL: @test_mm512_maskz_shldi_epi32
 118   // CHECK: @llvm.fshl.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> splat (i32 15))
 119   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
 120   return _mm512_maskz_shldi_epi32(__U, __A, __B, 15);
 121 }
 122
 123 __m512i test_mm512_shldi_epi32(__m512i __A, __m512i __B) {
 124   // CHECK-LABEL: @test_mm512_shldi_epi32
 125   // CHECK: @llvm.fshl.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> splat (i32 31))
 126   return _mm512_shldi_epi32(__A, __B, 31);
 127 }
 128
 129 __m512i test_mm512_mask_shldi_epi16(__m512i __S, __mmask32 __U, __m512i __A, __m512i __B) {
 130   // CHECK-LABEL: @test_mm512_mask_shldi_epi16
 131   // CHECK: @llvm.fshl.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> splat (i16 3))
 132   // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
 133   return _mm512_mask_shldi_epi16(__S, __U, __A, __B, 3);
 134 }
 135
 136 __m512i test_mm512_maskz_shldi_epi16(__mmask32 __U, __m512i __A, __m512i __B) {
 137   // CHECK-LABEL: @test_mm512_maskz_shldi_epi16
 138   // CHECK: @llvm.fshl.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> splat (i16 7))
 139   // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
 140   return _mm512_maskz_shldi_epi16(__U, __A, __B, 7);
 141 }
 142
 143 __m512i test_mm512_shldi_epi16(__m512i __A, __m512i __B) {
 144   // CHECK-LABEL: @test_mm512_shldi_epi16
 145   // CHECK: @llvm.fshl.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> splat (i16 15))
 146   return _mm512_shldi_epi16(__A, __B, 15);
 147 }
 148
 149 __m512i test_mm512_mask_shrdi_epi64(__m512i __S, __mmask8 __U, __m512i __A, __m512i __B) {
 150   // CHECK-LABEL: @test_mm512_mask_shrdi_epi64
 151   // CHECK: @llvm.fshr.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> splat (i64 47))
 152   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
 153   return _mm512_mask_shrdi_epi64(__S, __U, __A, __B, 47);
 154 }
 155
 156 __m512i test_mm512_maskz_shrdi_epi64(__mmask8 __U, __m512i __A, __m512i __B) {
 157   // CHECK-LABEL: @test_mm512_maskz_shrdi_epi64
 158   // CHECK: @llvm.fshr.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> splat (i64 63))
 159   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
 160   return _mm512_maskz_shrdi_epi64(__U, __A, __B, 63);
 161 }
 162
 163 __m512i test_mm512_shrdi_epi64(__m512i __A, __m512i __B) {
 164   // CHECK-LABEL: @test_mm512_shrdi_epi64
 165   // CHECK: @llvm.fshr.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> splat (i64 31))
 166   return _mm512_shrdi_epi64(__A, __B, 31);
 167 }
 168
 169 __m512i test_mm512_mask_shrdi_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) {
 170   // CHECK-LABEL: @test_mm512_mask_shrdi_epi32
 171   // CHECK: @llvm.fshr.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> splat (i32 7))
 172   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
 173   return _mm512_mask_shrdi_epi32(__S, __U, __A, __B, 7);
 174 }
 175
 176 __m512i test_mm512_maskz_shrdi_epi32(__mmask16 __U, __m512i __A, __m512i __B) {
 177   // CHECK-LABEL: @test_mm512_maskz_shrdi_epi32
 178   // CHECK: @llvm.fshr.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> splat (i32 15))
 179   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
 180   return _mm512_maskz_shrdi_epi32(__U, __A, __B, 15);
 181 }
 182
 183 __m512i test_mm512_shrdi_epi32(__m512i __A, __m512i __B) {
 184   // CHECK-LABEL: @test_mm512_shrdi_epi32
 185   // CHECK: @llvm.fshr.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> splat (i32 31))
 186   return _mm512_shrdi_epi32(__A, __B, 31);
 187 }
 188
 189 __m512i test_mm512_mask_shrdi_epi16(__m512i __S, __mmask32 __U, __m512i __A, __m512i __B) {
 190   // CHECK-LABEL: @test_mm512_mask_shrdi_epi16
 191   // CHECK: @llvm.fshr.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> splat (i16 3))
 192   // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
 193   return _mm512_mask_shrdi_epi16(__S, __U, __A, __B, 3);
 194 }
 195
 196 __m512i test_mm512_maskz_shrdi_epi16(__mmask32 __U, __m512i __A, __m512i __B) {
 197   // CHECK-LABEL: @test_mm512_maskz_shrdi_epi16
 198   // CHECK: @llvm.fshr.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> splat (i16 15))
 199   // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
 200   return _mm512_maskz_shrdi_epi16(__U, __A, __B, 15);
 201 }
 202
 203 __m512i test_mm512_shrdi_epi16(__m512i __A, __m512i __B) {
 204   // CHECK-LABEL: @test_mm512_shrdi_epi16
 205   // CHECK: @llvm.fshr.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> splat (i16 31))
 206   return _mm512_shrdi_epi16(__A, __B, 31);
 207 }
 208
 209 __m512i test_mm512_mask_shldv_epi64(__m512i __S, __mmask8 __U, __m512i __A, __m512i __B) {
 210   // CHECK-LABEL: @test_mm512_mask_shldv_epi64
 211   // CHECK: @llvm.fshl.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}})
 212   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
 213   return _mm512_mask_shldv_epi64(__S, __U, __A, __B);
 214 }
 215
 216 __m512i test_mm512_maskz_shldv_epi64(__mmask8 __U, __m512i __S, __m512i __A, __m512i __B) {
 217   // CHECK-LABEL: @test_mm512_maskz_shldv_epi64
 218   // CHECK: @llvm.fshl.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}})
 219   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
 220   return _mm512_maskz_shldv_epi64(__U, __S, __A, __B);
 221 }
 222
 223 __m512i test_mm512_shldv_epi64(__m512i __S, __m512i __A, __m512i __B) {
 224   // CHECK-LABEL: @test_mm512_shldv_epi64
 225   // CHECK: @llvm.fshl.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}})
 226   return _mm512_shldv_epi64(__S, __A, __B);
 227 }
 228
 229 __m512i test_mm512_mask_shldv_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) {
 230   // CHECK-LABEL: @test_mm512_mask_shldv_epi32
 231   // CHECK: @llvm.fshl.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}})
 232   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
 233   return _mm512_mask_shldv_epi32(__S, __U, __A, __B);
 234 }
 235
 236 __m512i test_mm512_maskz_shldv_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) {
 237   // CHECK-LABEL: @test_mm512_maskz_shldv_epi32
 238   // CHECK: @llvm.fshl.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}})
 239   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
 240   return _mm512_maskz_shldv_epi32(__U, __S, __A, __B);
 241 }
 242
 243 __m512i test_mm512_shldv_epi32(__m512i __S, __m512i __A, __m512i __B) {
 244   // CHECK-LABEL: @test_mm512_shldv_epi32
 245   // CHECK: @llvm.fshl.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}})
 246   return _mm512_shldv_epi32(__S, __A, __B);
 247 }
 248
 249 __m512i test_mm512_mask_shldv_epi16(__m512i __S, __mmask32 __U, __m512i __A, __m512i __B) {
 250   // CHECK-LABEL: @test_mm512_mask_shldv_epi16
 251   // CHECK: @llvm.fshl.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}})
 252   // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
 253   return _mm512_mask_shldv_epi16(__S, __U, __A, __B);
 254 }
 255
 256 __m512i test_mm512_maskz_shldv_epi16(__mmask32 __U, __m512i __S, __m512i __A, __m512i __B) {
 257   // CHECK-LABEL: @test_mm512_maskz_shldv_epi16
 258   // CHECK: @llvm.fshl.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}})
 259   // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
 260   return _mm512_maskz_shldv_epi16(__U, __S, __A, __B);
 261 }
 262
 263 __m512i test_mm512_shldv_epi16(__m512i __S, __m512i __A, __m512i __B) {
 264   // CHECK-LABEL: @test_mm512_shldv_epi16
 265   // CHECK: @llvm.fshl.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}})
 266   return _mm512_shldv_epi16(__S, __A, __B);
 267 }
 268
 269 __m512i test_mm512_mask_shrdv_epi64(__m512i __S, __mmask8 __U, __m512i __A, __m512i __B) {
 270   // CHECK-LABEL: @test_mm512_mask_shrdv_epi64
 271   // CHECK: @llvm.fshr.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}})
 272   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
 273   return _mm512_mask_shrdv_epi64(__S, __U, __A, __B);
 274 }
 275
 276 __m512i test_mm512_maskz_shrdv_epi64(__mmask8 __U, __m512i __S, __m512i __A, __m512i __B) {
 277   // CHECK-LABEL: @test_mm512_maskz_shrdv_epi64
 278   // CHECK: @llvm.fshr.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}})
 279   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
 280   return _mm512_maskz_shrdv_epi64(__U, __S, __A, __B);
 281 }
 282
 283 __m512i test_mm512_shrdv_epi64(__m512i __S, __m512i __A, __m512i __B) {
 284   // CHECK-LABEL: @test_mm512_shrdv_epi64
 285   // CHECK: @llvm.fshr.v8i64(<8 x i64> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}})
 286   return _mm512_shrdv_epi64(__S, __A, __B);
 287 }
 288
 289 __m512i test_mm512_mask_shrdv_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) {
 290   // CHECK-LABEL: @test_mm512_mask_shrdv_epi32
 291   // CHECK: @llvm.fshr.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}})
 292   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
 293   return _mm512_mask_shrdv_epi32(__S, __U, __A, __B);
 294 }
 295
 296 __m512i test_mm512_maskz_shrdv_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) {
 297   // CHECK-LABEL: @test_mm512_maskz_shrdv_epi32
 298   // CHECK: @llvm.fshr.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}})
 299   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
 300   return _mm512_maskz_shrdv_epi32(__U, __S, __A, __B);
 301 }
 302
 303 __m512i test_mm512_shrdv_epi32(__m512i __S, __m512i __A, __m512i __B) {
 304   // CHECK-LABEL: @test_mm512_shrdv_epi32
 305   // CHECK: @llvm.fshr.v16i32(<16 x i32> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}})
 306   return _mm512_shrdv_epi32(__S, __A, __B);
 307 }
 308
 309 __m512i test_mm512_mask_shrdv_epi16(__m512i __S, __mmask32 __U, __m512i __A, __m512i __B) {
 310   // CHECK-LABEL: @test_mm512_mask_shrdv_epi16
 311   // CHECK: @llvm.fshr.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}})
 312   // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
 313   return _mm512_mask_shrdv_epi16(__S, __U, __A, __B);
 314 }
 315
 316 __m512i test_mm512_maskz_shrdv_epi16(__mmask32 __U, __m512i __S, __m512i __A, __m512i __B) {
 317   // CHECK-LABEL: @test_mm512_maskz_shrdv_epi16
 318   // CHECK: @llvm.fshr.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}})
 319   // CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
 320   return _mm512_maskz_shrdv_epi16(__U, __S, __A, __B);
 321 }
 322
 323 __m512i test_mm512_shrdv_epi16(__m512i __S, __m512i __A, __m512i __B) {
 324   // CHECK-LABEL: @test_mm512_shrdv_epi16
 325   // CHECK: @llvm.fshr.v32i16(<32 x i16> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}})
 326   return _mm512_shrdv_epi16(__S, __A, __B);
 327 }
 328