[PATCH][i386,AVX] Enable VBMI2 support [2/7]

[Koval, Julia]

Hi,
This patch enables VPCOMPRESSB[W] instruction. The doc for isaset and instruction: https://software.intel.com/sites/default/files/managed/c5/15/architecture-instruction-set-extensions-programming-reference.pdf

Ok for trunk?

gcc/
	config.gcc (avx512vbmi2intrin.h, avx512vbmi2vlintrin): New headers.
	config/i386/avx512vbmi2intrin.h (_mm512_mask_compress_epi8,
	_mm512_maskz_compress_epi8, _mm512_mask_compressstoreu_epi8,
	_mm512_mask_compress_epi16, _mm512_maskz_compress_epi16,
	_mm512_mask_compressstoreu_epi16): New.
	config/i386/avx512vbmi2vlintrin.h (_mm_mask_compress_epi8,
	_mm_maskz_compress_epi8, _mm256_mask_compressstoreu_epi16,
	_mm_mask_compress_epi16, _mm_maskz_compress_epi16,
	_mm256_mask_compress_epi16, _mm256_maskz_compress_epi16,
	_mm_mask_compressstoreu_epi8, _mm_mask_compressstoreu_epi16,
	_mm256_mask_compress_epi8, _mm256_maskz_compress_epi8,
	_mm256_mask_compressstoreu_epi8): New.
	config/i386/i386-builtin-types.def (VOID_FTYPE_PV64QI_V64QI_UDI,
	VOID_FTYPE_PV32HI_V32HI_USI, VOID_FTYPE_PV32QI_V32QI_USI,
	VOID_FTYPE_PV16QI_V16QI_UHI, VOID_FTYPE_PV16HI_V16HI_UHI,
	VOID_FTYPE_PV8HI_V8HI_UQI): New types.
	config/i386/i386-builtin.def (__builtin_ia32_compressqi512_mask,
	__builtin_ia32_compresshi512_mask, __builtin_ia32_compressqi256_mask,
	__builtin_ia32_compressqi128_mask, __builtin_ia32_compresshi256_mask,
	__builtin_ia32_compresshi128_mask,
	__builtin_ia32_compressstoreuqi512_mask,
	__builtin_ia32_compressstoreuhi512_mask,
	__builtin_ia32_compressstoreuqi256_mask,
	__builtin_ia32_compressstoreuqi128_mask,
	__builtin_ia32_compressstoreuhi256_mask,
	__builtin_ia32_compressstoreuhi128_mask): New builtins.
	config/i386/i386.c (ix86_init_mmx_sse_builtins): Create special args
	array for flags2.
	(ix86_expand_special_args_builtin): Handle new types.
	(s4fma_expand): Handle new builtin array.
	config/i386/immintrin.h: Include new headers.
	config/i386/sse.md (VI12_AVX512VLBW): New iterator.
	(compress<mode>_mask, compressstore<mode>_mask): New patterns.

gcc/testsuite/
	gcc.target/i386/avx512-check.h: Handle AVX512VBMI2 bit.
	gcc.target/i386/avx512f-vpcompressb-1.c: New test.
	gcc.target/i386/avx512f-vpcompressb-2.c: Ditto.
	gcc.target/i386/avx512f-vpcompressw-1.c: Ditto.
	gcc.target/i386/avx512f-vpcompressw-2.c: Ditto.
	gcc.target/i386/avx512vl-vpcompressb-1.c: Ditto.
	gcc.target/i386/avx512vl-vpcompressb-2.c: Ditto.
	gcc.target/i386/avx512vl-vpcompressw-1.c: Ditto.
	gcc.target/i386/avx512vl-vpcompressw-2.c: Ditto.
	gcc.target/i386/i386.exp (check_effective_target_avx512vbmi2): New.
-------------- next part --------------
A non-text attachment was scrubbed...
Name: 0004-VPCOMPRESSB-W-instruction.patch
Type: application/octet-stream
Size: 32900 bytes
Desc: 0004-VPCOMPRESSB-W-instruction.patch
URL: <http://gcc.gnu.org/pipermail/gcc-patches/attachments/20171024/5f75f485/attachment.obj>