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

   1 // RUN: %clang_cc1 -flax-vector-conversions=none -ffreestanding %s -triple=x86_64-apple-darwin -target-feature +avx512vl -target-feature +avx512cd -emit-llvm -o - -Wall -Werror | FileCheck %s
   2
   3
   4 #include <immintrin.h>
   5
   6 __m128i test_mm_broadcastmb_epi64(__m128i a,__m128i b) {
   7   // CHECK-LABEL: @test_mm_broadcastmb_epi64
   8   // CHECK: icmp eq <4 x i32> %{{.*}}, %{{.*}}
   9   // CHECK: shufflevector <4 x i1> %{{.*}}, <4 x i1> zeroinitializer, <8 x i32> <i32 0, i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7>
  10   // CHECK: zext i8 %{{.*}} to i64
  11   // CHECK: insertelement <2 x i64> poison, i64 %{{.*}}, i32 0
  12   // CHECK: insertelement <2 x i64> %{{.*}}, i64 %{{.*}}, i32 1
  13   return _mm_broadcastmb_epi64(_mm_cmpeq_epi32_mask (a, b));
  14 }
  15
  16 __m256i test_mm256_broadcastmb_epi64(__m256i a, __m256i b) {
  17   // CHECK-LABEL: @test_mm256_broadcastmb_epi64
  18   // CHECK: icmp eq <4 x i64> %{{.*}}, %{{.*}}
  19   // CHECK: shufflevector <4 x i1> %{{.*}}, <4 x i1> zeroinitializer, <8 x i32> <i32 0, i32 1, i32 2, i32 3, i32 4, i32 5, i32 6, i32 7>
  20   // CHECK: zext i8 %{{.*}} to i64
  21   // CHECK: insertelement <4 x i64> poison, i64 %{{.*}}, i32 0
  22   // CHECK: insertelement <4 x i64> %{{.*}}, i64 %{{.*}}, i32 1
  23   // CHECK: insertelement <4 x i64> %{{.*}}, i64 %{{.*}}, i32 2
  24   // CHECK: insertelement <4 x i64> %{{.*}}, i64 %{{.*}}, i32 3
  25   return _mm256_broadcastmb_epi64(_mm256_cmpeq_epi64_mask ( a, b));
  26 }
  27
  28 __m128i test_mm_broadcastmw_epi32(__m512i a, __m512i b) {
  29   // CHECK-LABEL: @test_mm_broadcastmw_epi32
  30   // CHECK: icmp eq <16 x i32> %{{.*}}, %{{.*}}
  31   // CHECK: zext i16 %{{.*}} to i32
  32   // CHECK: insertelement <4 x i32> poison, i32 %{{.*}}, i32 0
  33   // CHECK: insertelement <4 x i32> %{{.*}}, i32 %{{.*}}, i32 1
  34   // CHECK: insertelement <4 x i32> %{{.*}}, i32 %{{.*}}, i32 2
  35   // CHECK: insertelement <4 x i32> %{{.*}}, i32 %{{.*}}, i32 3
  36   return _mm_broadcastmw_epi32(_mm512_cmpeq_epi32_mask ( a, b));
  37 }
  38
  39 __m256i test_mm256_broadcastmw_epi32(__m512i a, __m512i b) {
  40   // CHECK-LABEL: @test_mm256_broadcastmw_epi32
  41   // CHECK: icmp eq <16 x i32> %{{.*}}, %{{.*}}
  42   // CHECK: zext i16 %{{.*}} to i32
  43   // CHECK: insertelement <8 x i32> poison, i32 %{{.*}}, i32 0
  44   // CHECK: insertelement <8 x i32> %{{.*}}, i32 %{{.*}}, i32 1
  45   // CHECK: insertelement <8 x i32> %{{.*}}, i32 %{{.*}}, i32 2
  46   // CHECK: insertelement <8 x i32> %{{.*}}, i32 %{{.*}}, i32 3
  47   // CHECK: insertelement <8 x i32> %{{.*}}, i32 %{{.*}}, i32 4
  48   // CHECK: insertelement <8 x i32> %{{.*}}, i32 %{{.*}}, i32 5
  49   // CHECK: insertelement <8 x i32> %{{.*}}, i32 %{{.*}}, i32 6
  50   // CHECK: insertelement <8 x i32> %{{.*}}, i32 %{{.*}}, i32 7
  51   return _mm256_broadcastmw_epi32(_mm512_cmpeq_epi32_mask ( a, b));
  52 }
  53
  54 __m128i test_mm_conflict_epi64(__m128i __A) {
  55   // CHECK-LABEL: @test_mm_conflict_epi64
  56   // CHECK: @llvm.x86.avx512.conflict.q.128
  57   return _mm_conflict_epi64(__A);
  58 }
  59
  60 __m128i test_mm_mask_conflict_epi64(__m128i __W, __mmask8 __U, __m128i __A) {
  61   // CHECK-LABEL: @test_mm_mask_conflict_epi64
  62   // CHECK: @llvm.x86.avx512.conflict.q.128
  63   // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
  64   return _mm_mask_conflict_epi64(__W, __U, __A);
  65 }
  66
  67 __m128i test_mm_maskz_conflict_epi64(__mmask8 __U, __m128i __A) {
  68   // CHECK-LABEL: @test_mm_maskz_conflict_epi64
  69   // CHECK: @llvm.x86.avx512.conflict.q.128
  70   // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
  71   return _mm_maskz_conflict_epi64(__U, __A);
  72 }
  73
  74 __m256i test_mm256_conflict_epi64(__m256i __A) {
  75   // CHECK-LABEL: @test_mm256_conflict_epi64
  76   // CHECK: @llvm.x86.avx512.conflict.q.256
  77   return _mm256_conflict_epi64(__A);
  78 }
  79
  80 __m256i test_mm256_mask_conflict_epi64(__m256i __W, __mmask8 __U, __m256i __A) {
  81   // CHECK-LABEL: @test_mm256_mask_conflict_epi64
  82   // CHECK: @llvm.x86.avx512.conflict.q.256
  83   // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
  84   return _mm256_mask_conflict_epi64(__W, __U, __A);
  85 }
  86
  87 __m256i test_mm256_maskz_conflict_epi64(__mmask8 __U, __m256i __A) {
  88   // CHECK-LABEL: @test_mm256_maskz_conflict_epi64
  89   // CHECK: @llvm.x86.avx512.conflict.q.256
  90   // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
  91   return _mm256_maskz_conflict_epi64(__U, __A);
  92 }
  93
  94 __m128i test_mm_conflict_epi32(__m128i __A) {
  95   // CHECK-LABEL: @test_mm_conflict_epi32
  96   // CHECK: @llvm.x86.avx512.conflict.d.128
  97   return _mm_conflict_epi32(__A);
  98 }
  99
 100 __m128i test_mm_mask_conflict_epi32(__m128i __W, __mmask8 __U, __m128i __A) {
 101   // CHECK-LABEL: @test_mm_mask_conflict_epi32
 102   // CHECK: @llvm.x86.avx512.conflict.d.128
 103   // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
 104   return _mm_mask_conflict_epi32(__W, __U, __A);
 105 }
 106
 107 __m128i test_mm_maskz_conflict_epi32(__mmask8 __U, __m128i __A) {
 108   // CHECK-LABEL: @test_mm_maskz_conflict_epi32
 109   // CHECK: @llvm.x86.avx512.conflict.d.128
 110   // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
 111   return _mm_maskz_conflict_epi32(__U, __A);
 112 }
 113
 114 __m256i test_mm256_conflict_epi32(__m256i __A) {
 115   // CHECK-LABEL: @test_mm256_conflict_epi32
 116   // CHECK: @llvm.x86.avx512.conflict.d.256
 117   return _mm256_conflict_epi32(__A);
 118 }
 119
 120 __m256i test_mm256_mask_conflict_epi32(__m256i __W, __mmask8 __U, __m256i __A) {
 121   // CHECK-LABEL: @test_mm256_mask_conflict_epi32
 122   // CHECK: @llvm.x86.avx512.conflict.d.256
 123   // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
 124   return _mm256_mask_conflict_epi32(__W, __U, __A);
 125 }
 126
 127 __m256i test_mm256_maskz_conflict_epi32(__mmask8 __U, __m256i __A) {
 128   // CHECK-LABEL: @test_mm256_maskz_conflict_epi32
 129   // CHECK: @llvm.x86.avx512.conflict.d.256
 130   // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
 131   return _mm256_maskz_conflict_epi32(__U, __A);
 132 }
 133
 134 __m128i test_mm_lzcnt_epi32(__m128i __A) {
 135   // CHECK-LABEL: @test_mm_lzcnt_epi32
 136   // CHECK: call <4 x i32> @llvm.ctlz.v4i32(<4 x i32> %{{.*}}, i1 false)
 137   return _mm_lzcnt_epi32(__A);
 138 }
 139
 140 __m128i test_mm_mask_lzcnt_epi32(__m128i __W, __mmask8 __U, __m128i __A) {
 141   // CHECK-LABEL: @test_mm_mask_lzcnt_epi32
 142   // CHECK: call <4 x i32> @llvm.ctlz.v4i32(<4 x i32> %{{.*}}, i1 false)
 143   // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
 144   return _mm_mask_lzcnt_epi32(__W, __U, __A);
 145 }
 146
 147 __m128i test_mm_maskz_lzcnt_epi32(__mmask8 __U, __m128i __A) {
 148   // CHECK-LABEL: @test_mm_maskz_lzcnt_epi32
 149   // CHECK: call <4 x i32> @llvm.ctlz.v4i32(<4 x i32> %{{.*}}, i1 false)
 150   // CHECK: select <4 x i1> %{{.*}}, <4 x i32> %{{.*}}, <4 x i32> %{{.*}}
 151   return _mm_maskz_lzcnt_epi32(__U, __A);
 152 }
 153
 154 __m256i test_mm256_lzcnt_epi32(__m256i __A) {
 155   // CHECK-LABEL: @test_mm256_lzcnt_epi32
 156   // CHECK: call <8 x i32> @llvm.ctlz.v8i32(<8 x i32> %{{.*}}, i1 false)
 157   return _mm256_lzcnt_epi32(__A);
 158 }
 159
 160 __m256i test_mm256_mask_lzcnt_epi32(__m256i __W, __mmask8 __U, __m256i __A) {
 161   // CHECK-LABEL: @test_mm256_mask_lzcnt_epi32
 162   // CHECK: call <8 x i32> @llvm.ctlz.v8i32(<8 x i32> %{{.*}}, i1 false)
 163   // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
 164   return _mm256_mask_lzcnt_epi32(__W, __U, __A);
 165 }
 166
 167 __m256i test_mm256_maskz_lzcnt_epi32(__mmask8 __U, __m256i __A) {
 168   // CHECK-LABEL: @test_mm256_maskz_lzcnt_epi32
 169   // CHECK: call <8 x i32> @llvm.ctlz.v8i32(<8 x i32> %{{.*}}, i1 false)
 170   // CHECK: select <8 x i1> %{{.*}}, <8 x i32> %{{.*}}, <8 x i32> %{{.*}}
 171   return _mm256_maskz_lzcnt_epi32(__U, __A);
 172 }
 173
 174 __m128i test_mm_lzcnt_epi64(__m128i __A) {
 175   // CHECK-LABEL: @test_mm_lzcnt_epi64
 176   // CHECK: call <2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false)
 177   return _mm_lzcnt_epi64(__A);
 178 }
 179
 180 __m128i test_mm_mask_lzcnt_epi64(__m128i __W, __mmask8 __U, __m128i __A) {
 181   // CHECK-LABEL: @test_mm_mask_lzcnt_epi64
 182   // CHECK: call <2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false)
 183   // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
 184   return _mm_mask_lzcnt_epi64(__W, __U, __A);
 185 }
 186
 187 __m128i test_mm_maskz_lzcnt_epi64(__mmask8 __U, __m128i __A) {
 188   // CHECK-LABEL: @test_mm_maskz_lzcnt_epi64
 189   // CHECK: call <2 x i64> @llvm.ctlz.v2i64(<2 x i64> %{{.*}}, i1 false)
 190   // CHECK: select <2 x i1> %{{.*}}, <2 x i64> %{{.*}}, <2 x i64> %{{.*}}
 191   return _mm_maskz_lzcnt_epi64(__U, __A);
 192 }
 193
 194 __m256i test_mm256_lzcnt_epi64(__m256i __A) {
 195   // CHECK-LABEL: @test_mm256_lzcnt_epi64
 196   // CHECK: call <4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false)
 197   return _mm256_lzcnt_epi64(__A);
 198 }
 199
 200 __m256i test_mm256_mask_lzcnt_epi64(__m256i __W, __mmask8 __U, __m256i __A) {
 201   // CHECK-LABEL: @test_mm256_mask_lzcnt_epi64
 202   // CHECK: call <4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false)
 203   // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
 204   return _mm256_mask_lzcnt_epi64(__W, __U, __A);
 205 }
 206
 207 __m256i test_mm256_maskz_lzcnt_epi64(__mmask8 __U, __m256i __A) {
 208   // CHECK-LABEL: @test_mm256_maskz_lzcnt_epi64
 209   // CHECK: call <4 x i64> @llvm.ctlz.v4i64(<4 x i64> %{{.*}}, i1 false)
 210   // CHECK: select <4 x i1> %{{.*}}, <4 x i64> %{{.*}}, <4 x i64> %{{.*}}
 211   return _mm256_maskz_lzcnt_epi64(__U, __A);
 212 }