[Clang][AVX512] completing missing intrinsics [pandnd].

[AsafBadouh]

lib/Headers/avx512fintrin.h

402 ↗

(On Diff #56708)

I think it will be better to use:

return (__m512i)(~(__v8di)__A & (__v8di)__B);

[AsafBadouh]

LGTM

cfe/trunk/lib/Headers/avx512fintrin.h

_mm512_maskz_and_epi64(__mmask8 __k, __m512i __a, __m512i __b)
   return (__m512i) __builtin_ia32_pandq512_mask ((__v8di) __a,
               (__v8di) __b,
               (__v8di)
               _mm512_setzero_si512 (),
               (__mmask8) __k);
 }
 
 static __inline__ __m512i __DEFAULT_FN_ATTRS
+_mm512_andnot_si512 (__m512i __A, __m512i __B)
+{
+  return (__m512i)(~(__A) & __B);
+}
+
+static __inline__ __m512i __DEFAULT_FN_ATTRS
 _mm512_andnot_epi32 (__m512i __A, __m512i __B)
 {
   return (__m512i) __builtin_ia32_pandnd512_mask ((__v16si) __A,
               (__v16si) __B,
               (__v16si)
               _mm512_setzero_si512 (),
               (__mmask16) -1);
 }

cfe/trunk/test/CodeGen/avx512f-builtins.c

 
 __m512i test_mm512_mask_andnot_epi32 (__mmask16 __k,__m512i __A, __m512i __B,
                                       __m512i __src) {
   //CHECK-LABEL: @test_mm512_mask_andnot_epi32
   //CHECK: @llvm.x86.avx512.mask.pandn.d.512
   return _mm512_mask_andnot_epi32(__src,__k,__A,__B);
 }
 
+__m512i test_mm512_andnot_si512(__m512i __A, __m512i __B)
+{
+  //CHECK-LABLE: @test_mm512_andnot_si512
+  //CHECK: load {{.*}}%__A.addr.i, align 64
+  //CHECK: %neg.i = xor{{.*}}, <i64 -1, i64 -1, i64 -1, i64 -1, i64 -1, i64 -1, i64 -1, i64 -1>
+  //CHECK: load {{.*}}%__B.addr.i, align 64
+  //CHECK: and <8 x i64> %neg.i,{{.*}}
+
+  return _mm512_andnot_si512(__A, __B);
+}
+
 __m512i test_mm512_andnot_epi32(__m512i __A, __m512i __B) {
   //CHECK-LABEL: @test_mm512_andnot_epi32
   //CHECK: @llvm.x86.avx512.mask.pandn.d.512
   return _mm512_andnot_epi32(__A,__B);
 }
 
 __m512i test_mm512_maskz_andnot_epi64 (__mmask8 __k,__m512i __A, __m512i __B) {
   //CHECK-LABEL: @test_mm512_maskz_andnot_epi64