Instruction
VPCMPEQD
Compares packed doublewords for equality; the VEX form writes all-ones or zero elements, the EVEX form a mask register.
- Extensions
- Forms
- 10 (4 VEX, 6 EVEX)
- Data
- Intel XED v2026.08.23
Forms
| Instruction | Encoding | Requires |
|---|---|---|
VPCMPEQD xmm, xmm, m128
VPCMPEQD_XMMdq_XMMdq_MEMdq | VEX.128.66.0F.WIG 76 /r | AVX |
VPCMPEQD xmm, xmm, xmm
VPCMPEQD_XMMdq_XMMdq_XMMdq | VEX.128.66.0F.WIG 76 /r | AVX |
VPCMPEQD ymm, ymm, m256
VPCMPEQD_YMMqq_YMMqq_MEMqq | VEX.256.66.0F.WIG 76 /r | AVX2 |
VPCMPEQD ymm, ymm, ymm
VPCMPEQD_YMMqq_YMMqq_YMMqq | VEX.256.66.0F.WIG 76 /r | AVX2 |
VPCMPEQD k {k}, zmm, zmm
VPCMPEQD_MASKmskw_MASKmskw_ZMMu32_ZMMu32_AVX512 | EVEX.512.66.0F.W0 76 /r | AVX10.1 or AVX512F |
VPCMPEQD k {k}, zmm, m512/m32bcst
VPCMPEQD_MASKmskw_MASKmskw_ZMMu32_MEMu32_AVX512 | EVEX.512.66.0F.W0 76 /r | AVX10.1 or AVX512F |
VPCMPEQD k {k}, xmm, xmm
VPCMPEQD_MASKmskw_MASKmskw_XMMu32_XMMu32_AVX512 | EVEX.128.66.0F.W0 76 /r | AVX10.1 or AVX512F + AVX512VL |
VPCMPEQD k {k}, xmm, m128/m32bcst
VPCMPEQD_MASKmskw_MASKmskw_XMMu32_MEMu32_AVX512 | EVEX.128.66.0F.W0 76 /r | AVX10.1 or AVX512F + AVX512VL |
VPCMPEQD k {k}, ymm, ymm
VPCMPEQD_MASKmskw_MASKmskw_YMMu32_YMMu32_AVX512 | EVEX.256.66.0F.W0 76 /r | AVX10.1 or AVX512F + AVX512VL |
VPCMPEQD k {k}, ymm, m256/m32bcst
VPCMPEQD_MASKmskw_MASKmskw_YMMu32_MEMu32_AVX512 | EVEX.256.66.0F.W0 76 /r | AVX10.1 or AVX512F + AVX512VL |
Intrinsics
The C intrinsics of Clang 23.1.2 that compile to VPCMPEQD, each with the form it compiles to and the Clang options it needs. The forms come from compiling every intrinsic and decoding the result with Intel XED; all intrinsics A–Z explains the method.
| Intrinsic | Compiles to |
|---|---|
_mm_cmpeq_epi32
__m128i _mm_cmpeq_epi32(__m128i __a, __m128i __b) |
|
_mm_cmpeq_epi32_mask
__mmask8 _mm_cmpeq_epi32_mask(__m128i A, __m128i B) |
|
_mm_cmpeq_epu32_mask
__mmask8 _mm_cmpeq_epu32_mask(__m128i A, __m128i B) |
|
_mm_mask_cmpeq_epi32_mask
__mmask8 _mm_mask_cmpeq_epi32_mask(__mmask8 k, __m128i A, __m128i B) |
|
_mm_mask_cmpeq_epu32_mask
__mmask8 _mm_mask_cmpeq_epu32_mask(__mmask8 k, __m128i A, __m128i B) |
|
_mm256_cmpeq_epi32
__m256i _mm256_cmpeq_epi32(__m256i __a, __m256i __b) |
|
_mm256_cmpeq_epi32_mask
__mmask8 _mm256_cmpeq_epi32_mask(__m256i A, __m256i B) |
|
_mm256_mask_cmpeq_epi32_mask
__mmask8 _mm256_mask_cmpeq_epi32_mask(__mmask8 k, __m256i A, __m256i B) |
|
_mm256_cmpeq_epu32_mask
__mmask8 _mm256_cmpeq_epu32_mask(__m256i A, __m256i B) |
|
_mm256_mask_cmpeq_epu32_mask
__mmask8 _mm256_mask_cmpeq_epu32_mask(__mmask8 k, __m256i A, __m256i B) |
|
_mm512_cmpeq_epi32_mask
__mmask16 _mm512_cmpeq_epi32_mask(__m512i A, __m512i B) |
|
_mm512_mask_cmpeq_epi32_mask
__mmask16 _mm512_mask_cmpeq_epi32_mask(__mmask16 k, __m512i A, __m512i B) |
|
_mm512_cmpeq_epu32_mask
__mmask16 _mm512_cmpeq_epu32_mask(__m512i A, __m512i B) |
|
_mm512_mask_cmpeq_epu32_mask
__mmask16 _mm512_mask_cmpeq_epu32_mask(__mmask16 k, __m512i A, __m512i B) |
|
CPUID and processors
Each form belongs to an XED ISA set. A form can be used when the processor reports every CPUID bit of one of its ISA set's alternatives.
More AVX10.1 instructions
- VPANDD
- VPANDND
- VPANDNQ
- VPANDQ
- VPAVGB
- VPAVGW
- VPBLENDMB
- VPBLENDMD
- VPBLENDMQ
- VPBLENDMW
- VPBROADCASTB
- VPBROADCASTD
- VPBROADCASTMB2Q
- VPBROADCASTMW2D
- VPBROADCASTQ
- VPBROADCASTW
- VPCLMULQDQ
- VPCMPB
- VPCMPD
- VPCMPEQB
- VPCMPEQQ
- VPCMPEQW
- VPCMPGTB
- VPCMPGTD
- VPCMPGTQ
- VPCMPGTW
- VPCMPQ
- VPCMPUB
- VPCMPUD
- VPCMPUQ
- VPCMPUW
- VPCMPW
- VPCOMPRESSB
- VPCOMPRESSD
- VPCOMPRESSQ
- VPCOMPRESSW
- VPCONFLICTD
- VPCONFLICTQ
- VPDPBUSD
- VPDPBUSDS
Sources
- Intel XED v2026.08.23 (commit
0bcb6237345c): forms, encodings, ISA sets, CPUID bits and chip model. - Clang's x86 intrinsic headers, LLVM 23.1.2 (commit
85ac56026243): the intrinsics, their signatures and doc comments, and the Clang of that release, which compiled each of them. - Intel Advanced Vector Extensions 10.2 Architecture Specification, revision 6.0 (361050-006, January 2026)
The tables are derived from Intel XED, Copyright Intel Corporation, licensed under the Apache License 2.0; x86-64.net converted and reformatted them. The intrinsics and their signatures come from Clang, part of the LLVM Project, licensed under the Apache License 2.0 with LLVM Exceptions. The text is our own.