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

   1 // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s
   2
   3
   4 #include <immintrin.h>
   5
   6 __m512i test_mm512_conflict_epi64(__m512i __A) {
   7   // CHECK-LABEL: @test_mm512_conflict_epi64
   8   // CHECK: @llvm.x86.avx512.conflict.q.512
   9   return _mm512_conflict_epi64(__A);
  10 }
  11 __m512i test_mm512_mask_conflict_epi64(__m512i __W, __mmask8 __U, __m512i __A) {
  12   // CHECK-LABEL: @test_mm512_mask_conflict_epi64
  13   // CHECK: @llvm.x86.avx512.conflict.q.512
  14   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
  15   return _mm512_mask_conflict_epi64(__W,__U,__A);
  16 }
  17 __m512i test_mm512_maskz_conflict_epi64(__mmask8 __U, __m512i __A) {
  18   // CHECK-LABEL: @test_mm512_maskz_conflict_epi64
  19   // CHECK: @llvm.x86.avx512.conflict.q.512
  20   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
  21   return _mm512_maskz_conflict_epi64(__U,__A);
  22 }
  23 __m512i test_mm512_conflict_epi32(__m512i __A) {
  24   // CHECK-LABEL: @test_mm512_conflict_epi32
  25   // CHECK: @llvm.x86.avx512.conflict.d.512
  26   return _mm512_conflict_epi32(__A);
  27 }
  28 __m512i test_mm512_mask_conflict_epi32(__m512i __W, __mmask16 __U, __m512i __A) {
  29   // CHECK-LABEL: @test_mm512_mask_conflict_epi32
  30   // CHECK: @llvm.x86.avx512.conflict.d.512
  31   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  32   return _mm512_mask_conflict_epi32(__W,__U,__A);
  33 }
  34 __m512i test_mm512_maskz_conflict_epi32(__mmask16 __U, __m512i __A) {
  35   // CHECK-LABEL: @test_mm512_maskz_conflict_epi32
  36   // CHECK: @llvm.x86.avx512.conflict.d.512
  37   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  38   return _mm512_maskz_conflict_epi32(__U,__A);
  39 }
  40 __m512i test_mm512_lzcnt_epi32(__m512i __A) {
  41   // CHECK-LABEL: @test_mm512_lzcnt_epi32
  42   // CHECK: call <16 x i32> @llvm.ctlz.v16i32(<16 x i32> %{{.*}}, i1 false)
  43   return _mm512_lzcnt_epi32(__A);
  44 }
  45 __m512i test_mm512_mask_lzcnt_epi32(__m512i __W, __mmask16 __U, __m512i __A) {
  46   // CHECK-LABEL: @test_mm512_mask_lzcnt_epi32
  47   // CHECK: call <16 x i32> @llvm.ctlz.v16i32(<16 x i32> %{{.*}}, i1 false)
  48   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  49   return _mm512_mask_lzcnt_epi32(__W,__U,__A);
  50 }
  51 __m512i test_mm512_maskz_lzcnt_epi32(__mmask16 __U, __m512i __A) {
  52   // CHECK-LABEL: @test_mm512_maskz_lzcnt_epi32
  53   // CHECK: call <16 x i32> @llvm.ctlz.v16i32(<16 x i32> %{{.*}}, i1 false)
  54   // CHECK: select <16 x i1> %{{.*}}, <16 x i32> %{{.*}}, <16 x i32> %{{.*}}
  55   return _mm512_maskz_lzcnt_epi32(__U,__A);
  56 }
  57 __m512i test_mm512_lzcnt_epi64(__m512i __A) {
  58   // CHECK-LABEL: @test_mm512_lzcnt_epi64
  59   // CHECK: call <8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false)
  60   return _mm512_lzcnt_epi64(__A);
  61 }
  62 __m512i test_mm512_mask_lzcnt_epi64(__m512i __W, __mmask8 __U, __m512i __A) {
  63   // CHECK-LABEL: @test_mm512_mask_lzcnt_epi64
  64   // CHECK: call <8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false)
  65   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
  66   return _mm512_mask_lzcnt_epi64(__W,__U,__A);
  67 }
  68 __m512i test_mm512_maskz_lzcnt_epi64(__mmask8 __U, __m512i __A) {
  69   // CHECK-LABEL: @test_mm512_maskz_lzcnt_epi64
  70   // CHECK: call <8 x i64> @llvm.ctlz.v8i64(<8 x i64> %{{.*}}, i1 false)
  71   // CHECK: select <8 x i1> %{{.*}}, <8 x i64> %{{.*}}, <8 x i64> %{{.*}}
  72   return _mm512_maskz_lzcnt_epi64(__U,__A);
  73 }
  74
  75 __m512i test_mm512_broadcastmb_epi64(__m512i a, __m512i b) {
  76   // CHECK-LABEL: @test_mm512_broadcastmb_epi64
  77   // CHECK: icmp eq <8 x i64> %{{.*}}, %{{.*}}
  78   // CHECK: zext i8 %{{.*}} to i64
  79   // CHECK: insertelement <8 x i64> poison, i64 %{{.*}}, i32 0
  80   // CHECK: insertelement <8 x i64> %{{.*}}, i64 %{{.*}}, i32 1
  81   // CHECK: insertelement <8 x i64> %{{.*}}, i64 %{{.*}}, i32 2
  82   // CHECK: insertelement <8 x i64> %{{.*}}, i64 %{{.*}}, i32 3
  83   // CHECK: insertelement <8 x i64> %{{.*}}, i64 %{{.*}}, i32 4
  84   // CHECK: insertelement <8 x i64> %{{.*}}, i64 %{{.*}}, i32 5
  85   // CHECK: insertelement <8 x i64> %{{.*}}, i64 %{{.*}}, i32 6
  86   // CHECK: insertelement <8 x i64> %{{.*}}, i64 %{{.*}}, i32 7
  87   return _mm512_broadcastmb_epi64(_mm512_cmpeq_epu64_mask ( a, b));
  88 }
  89
  90 __m512i test_mm512_broadcastmw_epi32(__m512i a, __m512i b) {
  91   // CHECK-LABEL: @test_mm512_broadcastmw_epi32
  92   // CHECK: icmp eq <16 x i32> %{{.*}}, %{{.*}}
  93   // CHECK: zext i16 %{{.*}} to i32
  94   // CHECK: insertelement <16 x i32> poison, i32 %{{.*}}
  95   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
  96   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
  97   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
  98   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
  99   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 100   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 101   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 102   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 103   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 104   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 105   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 106   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 107   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 108   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 109   // CHECK: insertelement <16 x i32> %{{.*}}, i32 %{{.*}}
 110   return _mm512_broadcastmw_epi32(_mm512_cmpeq_epi32_mask ( a, b));
 111 }