VPSHLDQ - Packed SHift Left Double Qword

VPSHLDQ xmm1{k1}{z}, xmm2, xmm3/m128/m64bcst, imm8    (V5+VBMI2+VL
__m128i _mm_shldi_epi64(__m128i a, __m128i b, int imm8)
__m128i _mm_mask_shldi_epi64(__m128i s, __mmask8 k, __m128i a, __m128i b, int imm8)
__m128i _mm_maskz_shldi_epi64(__mmask8 k, __m128i a, __m128i b, int imm8)

For each QWORD, (1) is shifted to the left by the number of bits specified in imm8 bit 5:0. Upper bits of (2) are copied to the emptied lower bits. The result is stored in (3).
VPSHLDQ ymm1{k1}{z}, ymm2, ymm3/m256/m64bcst, imm8    (V5+VBMI2+VL
__m256i _mm256_shldi_epi64(__m256i a, __m256i b, int imm8)
__m256i _mm256_mask_shldi_epi64(__m256i s, __mmask8 k, __m256i a, __m256i b, int imm8)
__m256i _mm256_maskz_shldi_epi64(__mmask8 k, __m256i a, __m256i b, int imm8)

For each QWORD, (1) is shifted to the left by the number of bits specified in imm8 bit 5:0. Upper bits of (2) are copied to the emptied lower bits. The result is stored in (3).
VPSHLDQ zmm1{k1}{z}, zmm2, zmm3/m512/m64bcst, imm8    (V5+VBMI2
__m512i _mm512_shldi_epi64(__m512i a, __m512i b, int imm8)
__m512i _mm512_mask_shldi_epi64(__m512i s, __mmask8 k, __m512i a, __m512i b, int imm8)
__m512i _mm512_maskz_shldi_epi64(__mmask8 k, __m512i a, __m512i b, int imm8)

For each QWORD, (1) is shifted to the left by the number of bits specified in imm8 bit 5:0. Upper bits of (2) are copied to the emptied lower bits. The result is stored in (3).

x86/x64 SIMD Instruction List  Feedback