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

[AsafBadouh]

LGTM

cfe/trunk/lib/Headers/avx512fintrin.h

#define _mm512_maskz_alignr_epi32( __U, __A, __B, __imm) __extension__({\
     (__m512i) __builtin_ia32_alignd512_mask ((__v16si) __A,\
                                          (__v16si) __B, __imm,\
                                          (__v16si) _mm512_setzero_si512 (),\
                                          (__mmask16) __U);\
 })
 /* Vector Extract */
 
 #define _mm512_extractf64x4_pd(A, I) __extension__ ({                    \
-      (__m256d)                                                          \
-        __builtin_ia32_extractf64x4_mask((__v8df)(__m512d)(A),           \
+      (__m256d) __builtin_ia32_extractf64x4_mask((__v8df)(__m512d)(A),   \
                                          (I),                            \
                                          (__v4df)_mm256_setzero_si256(), \
                                          (__mmask8) -1); })
 
+#define _mm512_mask_extractf64x4_pd( __W, __U, __A, __imm) __extension__ ({\
+      (__m256d) __builtin_ia32_extractf64x4_mask ((__v8df) __A, \
+                                         __imm,\
+                                         (__v4df) __W,\
+                                         (__mmask8) __U);\
+})
+
+#define _mm512_maskz_extractf64x4_pd( __U, __A, __imm) __extension__ ({\
+      (__m256d) __builtin_ia32_extractf64x4_mask ((__v8df) __A,\
+                                         __imm,\
+                                         (__v4df)\
+                                         _mm256_setzero_pd (),\
+                                         (__mmask8) __U);\
+})
+
 #define _mm512_extractf32x4_ps(A, I) __extension__ ({                    \
-      (__m128)                                                           \
-        __builtin_ia32_extractf32x4_mask((__v16sf)(__m512)(A),           \
+      (__m128) __builtin_ia32_extractf32x4_mask((__v16sf)(__m512)(A),    \
                                          (I),                            \
                                          (__v4sf)_mm_setzero_ps(),       \
                                          (__mmask8) -1); })
 
+#define _mm512_mask_extractf32x4_ps( __W, __U, __A, __imm) __extension__ ({\
+      (__m128) __builtin_ia32_extractf32x4_mask ((__v16sf) __A,\
+                                         __imm,\
+                                         (__v4sf) __W,\
+                                         (__mmask8) __U);\
+})
+
+#define _mm512_maskz_extractf32x4_ps( __U, __A, __imm) __extension__ ({\
+      (__m128) __builtin_ia32_extractf32x4_mask ((__v16sf) __A,\
+                                         __imm,\
+                                         (__v4sf)\
+                                         _mm_setzero_ps (),\
+                                         (__mmask8) __U);\
+})
 /* Vector Blend */
 
 static __inline __m512d __DEFAULT_FN_ATTRS
 _mm512_mask_blend_pd(__mmask8 __U, __m512d __A, __m512d __W)
 {
   return (__m512d) __builtin_ia32_blendmpd_512_mask ((__v8df) __A,
                  (__v8df) __W,
                  (__mmask8) __U);

 static __inline__ __m256 __DEFAULT_FN_ATTRS
 _mm512_maskz_cvtpd_ps (__mmask8 __U, __m512d __A)
 {
   return (__m256) __builtin_ia32_cvtpd2ps512_mask ((__v8df) __A,
                 (__v8sf) _mm256_setzero_ps (),
                 (__mmask8) __U,
                 _MM_FROUND_CUR_DIRECTION);
 }
-                                          
 #define _mm512_cvtps_ph(A, I) __extension__ ({ \
   (__m256i)__builtin_ia32_vcvtps2ph512_mask((__v16sf)(A), (I), \
                                             (__v16hi)_mm256_setzero_si256(), \
                                             -1); })
 
 #define _mm512_mask_cvtps_ph(__U, __W, __A, __I) __extension__ ({ \
   (__m256i) __builtin_ia32_vcvtps2ph512_mask((__v16sf) __A,\
                   __I,\
#define _mm512_cvtt_roundpd_epi32(A, R) __extension__ ({ \
   (__m256i)__builtin_ia32_cvttpd2dq512_mask((__v8df)(A), \
                                             (__v8si)_mm256_setzero_si256(), \
                                             (__mmask8)-1, (R)); })
 
 #define _mm512_cvtt_roundps_epi32(A, R) __extension__ ({ \
   (__m512i)__builtin_ia32_cvttps2dq512_mask((__v16sf)(A), \
                                             (__v16si)_mm512_setzero_si512(), \
                                             (__mmask16)-1, (R)); })
-                                            
 static __inline __m512i __DEFAULT_FN_ATTRS
 _mm512_cvttps_epi32(__m512 __a)
 {
   return (__m512i)
     __builtin_ia32_cvttps2dq512_mask((__v16sf) __a,
                                      (__v16si) _mm512_setzero_si512 (),
                                      (__mmask16) -1, _MM_FROUND_CUR_DIRECTION);
 }

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

 
 __m256d test_mm512_extractf64x4_pd(__m512d a)
 {
   // CHECK-LABEL: @test_mm512_extractf64x4_pd
   // CHECK: @llvm.x86.avx512.mask.vextractf64x4.512
   return _mm512_extractf64x4_pd(a, 1);
 }
 
+__m256d test_mm512_mask_extractf64x4_pd(__m256d  __W,__mmask8  __U,__m512d __A){
+ //CHECK-LABLE:@test_mm512_mask_extractf64x4_pd
+ //CHECL:@llvm.x86.avx512.mask.vextractf64x4.512
+ return _mm512_mask_extractf64x4_pd( __W, __U, __A, 1);
+}
+
+__m256d test_mm512_maskz_extractf64x4_pd(__mmask8  __U,__m512d __A){
+ //CHECK-LABLE:@test_mm512_maskz_extractf64x4_pd
+ //CHECL:@llvm.x86.avx512.mask.vextractf64x4.512
+ return _mm512_maskz_extractf64x4_pd( __U, __A, 1);
+}
+
 __m128 test_mm512_extractf32x4_ps(__m512 a)
 {
   // CHECK-LABEL: @test_mm512_extractf32x4_ps
   // CHECK: @llvm.x86.avx512.mask.vextractf32x4.512
   return _mm512_extractf32x4_ps(a, 1);
 }
 
+__m128 test_mm512_mask_extractf32x4_ps(__m128 __W, __mmask8  __U,__m512d __A){
+ //CHECK-LABLE:@test_mm512_mask_extractf32x4_ps
+ //CHECL: @llvm.x86.avx512.mask.vextractf32x4.512
+ return _mm512_mask_extractf32x4_ps( __W, __U, __A, 1);
+}
+
+__m128 test_mm512_maskz_extractf32x4_ps( __mmask8  __U,__m512d __A){
+ //CHECK-LABLE:@test_mm512_maskz_extractf32x4_ps
+ //CHECL: @llvm.x86.avx512.mask.vextractf32x4.512
+ return _mm512_maskz_extractf32x4_ps(  __U, __A, 1);
+}
+
 __mmask16 test_mm512_cmpeq_epu32_mask(__m512i __a, __m512i __b) {
   // CHECK-LABEL: @test_mm512_cmpeq_epu32_mask
   // CHECK: @llvm.x86.avx512.mask.ucmp.d.512(<16 x i32> {{.*}}, <16 x i32> {{.*}}, i32 0, i16 -1)
   return (__mmask16)_mm512_cmpeq_epu32_mask(__a, __b);
 }
 
 __mmask16 test_mm512_mask_cmpeq_epu32_mask(__mmask16 __u, __m512i __a, __m512i __b) {
   // CHECK-LABEL: @test_mm512_mask_cmpeq_epu32_mask