Instruction
VPADDUSW
Adds packed unsigned words with unsigned saturation.
- Extensions
- Forms
- 10 (4 VEX, 6 EVEX)
- Data
- Intel XED v2026.08.23
Forms
| Instruction | Encoding | Requires |
|---|---|---|
VPADDUSW xmm, xmm, m128
VPADDUSW_XMMdq_XMMdq_MEMdq | VEX.128.66.0F.WIG DD /r | AVX |
VPADDUSW xmm, xmm, xmm
VPADDUSW_XMMdq_XMMdq_XMMdq | VEX.128.66.0F.WIG DD /r | AVX |
VPADDUSW ymm, ymm, m256
VPADDUSW_YMMqq_YMMqq_MEMqq | VEX.256.66.0F.WIG DD /r | AVX2 |
VPADDUSW ymm, ymm, ymm
VPADDUSW_YMMqq_YMMqq_YMMqq | VEX.256.66.0F.WIG DD /r | AVX2 |
VPADDUSW xmm {k}{z}, xmm, xmm
VPADDUSW_XMMu16_MASKmskw_XMMu16_XMMu16_AVX512 | EVEX.128.66.0F.WIG DD /r | AVX10.1 or AVX512BW + AVX512VL |
VPADDUSW xmm {k}{z}, xmm, m128
VPADDUSW_XMMu16_MASKmskw_XMMu16_MEMu16_AVX512 | EVEX.128.66.0F.WIG DD /r | AVX10.1 or AVX512BW + AVX512VL |
VPADDUSW ymm {k}{z}, ymm, ymm
VPADDUSW_YMMu16_MASKmskw_YMMu16_YMMu16_AVX512 | EVEX.256.66.0F.WIG DD /r | AVX10.1 or AVX512BW + AVX512VL |
VPADDUSW ymm {k}{z}, ymm, m256
VPADDUSW_YMMu16_MASKmskw_YMMu16_MEMu16_AVX512 | EVEX.256.66.0F.WIG DD /r | AVX10.1 or AVX512BW + AVX512VL |
VPADDUSW zmm {k}{z}, zmm, zmm
VPADDUSW_ZMMu16_MASKmskw_ZMMu16_ZMMu16_AVX512 | EVEX.512.66.0F.WIG DD /r | AVX10.1 or AVX512BW |
VPADDUSW zmm {k}{z}, zmm, m512
VPADDUSW_ZMMu16_MASKmskw_ZMMu16_MEMu16_AVX512 | EVEX.512.66.0F.WIG DD /r | AVX10.1 or AVX512BW |
Intrinsics
The C intrinsics of Clang 23.1.2 that compile to VPADDUSW, 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_adds_epu16
__m128i _mm_adds_epu16(__m128i __a, __m128i __b) |
Clang's comment names VPADDUSB, the byte addition; this intrinsic adds unsigned words with saturation, and Clang emits PADDUSW or VPADDUSW. |
_mm_mask_adds_epu16
__m128i _mm_mask_adds_epu16(__m128i __W, __mmask8 __U, __m128i __A, __m128i __B) |
|
_mm_maskz_adds_epu16
__m128i _mm_maskz_adds_epu16(__mmask8 __U, __m128i __A, __m128i __B) |
|
_mm256_adds_epu16
__m256i _mm256_adds_epu16(__m256i __a, __m256i __b) |
|
_mm256_mask_adds_epu16
__m256i _mm256_mask_adds_epu16(__m256i __W, __mmask16 __U, __m256i __A, __m256i __B) |
|
_mm256_maskz_adds_epu16
__m256i _mm256_maskz_adds_epu16(__mmask16 __U, __m256i __A, __m256i __B) |
|
_mm512_adds_epu16
__m512i _mm512_adds_epu16(__m512i __A, __m512i __B) |
|
_mm512_mask_adds_epu16
__m512i _mm512_mask_adds_epu16(__m512i __W, __mmask32 __U, __m512i __A, __m512i __B) |
|
_mm512_maskz_adds_epu16
__m512i _mm512_maskz_adds_epu16(__mmask32 __U, __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
- VMULPS
- VMULSD
- VMULSH
- VMULSS
- VORPD
- VORPS
- VPABSB
- VPABSD
- VPABSQ
- VPABSW
- VPACKSSDW
- VPACKSSWB
- VPACKUSDW
- VPACKUSWB
- VPADDB
- VPADDD
- VPADDQ
- VPADDSB
- VPADDSW
- VPADDUSB
- VPADDW
- VPALIGNR
- VPANDD
- VPANDND
- VPANDNQ
- VPANDQ
- VPAVGB
- VPAVGW
- VPBLENDMB
- VPBLENDMD
- VPBLENDMQ
- VPBLENDMW
- VPBROADCASTB
- VPBROADCASTD
- VPBROADCASTMB2Q
- VPBROADCASTMW2D
- VPBROADCASTQ
- VPBROADCASTW
- VPCLMULQDQ
- VPCMPB
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.