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

   1 //  RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vnni -emit-llvm -o - -Wall -Werror | FileCheck %s
   2
   3 #include <immintrin.h>
   4
   5 __m512i test_mm512_mask_dpbusd_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) {
   6   // CHECK-LABEL: @test_mm512_mask_dpbusd_epi32
   7   // CHECK: @llvm.x86.avx512.vpdpbusd.512
   8   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
   9   return _mm512_mask_dpbusd_epi32(__S, __U, __A, __B);
  10 }
  11
  12 __m512i test_mm512_maskz_dpbusd_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) {
  13   // CHECK-LABEL: @test_mm512_maskz_dpbusd_epi32
  14   // CHECK: @llvm.x86.avx512.vpdpbusd.512
  15   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  16   return _mm512_maskz_dpbusd_epi32(__U, __S, __A, __B);
  17 }
  18
  19 __m512i test_mm512_dpbusd_epi32(__m512i __S, __m512i __A, __m512i __B) {
  20   // CHECK-LABEL: @test_mm512_dpbusd_epi32
  21   // CHECK: @llvm.x86.avx512.vpdpbusd.512
  22   return _mm512_dpbusd_epi32(__S, __A, __B);
  23 }
  24
  25 __m512i test_mm512_mask_dpbusds_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) {
  26   // CHECK-LABEL: @test_mm512_mask_dpbusds_epi32
  27   // CHECK: @llvm.x86.avx512.vpdpbusds.51
  28   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  29   return _mm512_mask_dpbusds_epi32(__S, __U, __A, __B);
  30 }
  31
  32 __m512i test_mm512_maskz_dpbusds_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) {
  33   // CHECK-LABEL: @test_mm512_maskz_dpbusds_epi32
  34   // CHECK: @llvm.x86.avx512.vpdpbusds.512
  35   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  36   return _mm512_maskz_dpbusds_epi32(__U, __S, __A, __B);
  37 }
  38
  39 __m512i test_mm512_dpbusds_epi32(__m512i __S, __m512i __A, __m512i __B) {
  40   // CHECK-LABEL: @test_mm512_dpbusds_epi32
  41   // CHECK: @llvm.x86.avx512.vpdpbusds.512
  42   return _mm512_dpbusds_epi32(__S, __A, __B);
  43 }
  44
  45 __m512i test_mm512_mask_dpwssd_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) {
  46   // CHECK-LABEL: @test_mm512_mask_dpwssd_epi32
  47   // CHECK: @llvm.x86.avx512.vpdpwssd.512
  48   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  49   return _mm512_mask_dpwssd_epi32(__S, __U, __A, __B);
  50 }
  51
  52 __m512i test_mm512_maskz_dpwssd_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) {
  53   // CHECK-LABEL: @test_mm512_maskz_dpwssd_epi32
  54   // CHECK: @llvm.x86.avx512.vpdpwssd.512
  55   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  56   return _mm512_maskz_dpwssd_epi32(__U, __S, __A, __B);
  57 }
  58
  59 __m512i test_mm512_dpwssd_epi32(__m512i __S, __m512i __A, __m512i __B) {
  60   // CHECK-LABEL: @test_mm512_dpwssd_epi32
  61   // CHECK: @llvm.x86.avx512.vpdpwssd.512
  62   return _mm512_dpwssd_epi32(__S, __A, __B);
  63 }
  64
  65 __m512i test_mm512_mask_dpwssds_epi32(__m512i __S, __mmask16 __U, __m512i __A, __m512i __B) {
  66   // CHECK-LABEL: @test_mm512_mask_dpwssds_epi32
  67   // CHECK: @llvm.x86.avx512.vpdpwssds.512
  68   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  69   return _mm512_mask_dpwssds_epi32(__S, __U, __A, __B);
  70 }
  71
  72 __m512i test_mm512_maskz_dpwssds_epi32(__mmask16 __U, __m512i __S, __m512i __A, __m512i __B) {
  73   // CHECK-LABEL: @test_mm512_maskz_dpwssds_epi32
  74   // CHECK: @llvm.x86.avx512.vpdpwssds.512
  75   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  76   return _mm512_maskz_dpwssds_epi32(__U, __S, __A, __B);
  77 }
  78
  79 __m512i test_mm512_dpwssds_epi32(__m512i __S, __m512i __A, __m512i __B) {
  80   // CHECK-LABEL: @test_mm512_dpwssds_epi32
  81   // CHECK: @llvm.x86.avx512.vpdpwssds.512
  82   return _mm512_dpwssds_epi32(__S, __A, __B);
  83 }
  84