Instruction
VFPCLASSPH
Tests packed half-precision values for the classes an immediate selects, such as NaN, zero or infinity, and writes the results to a mask register.
- Extensions
- Forms
- 6 (6 EVEX)
- Data
- Intel XED v2026.08.23
Forms
| Instruction | Encoding | Requires |
|---|---|---|
VFPCLASSPH k {k}, xmm, imm8
VFPCLASSPH_MASKmskw_MASKmskw_XMMf16_IMM8_AVX512 | EVEX.128.NP.0F3A.W0 66 /r ib | AVX10.1 or AVX512_FP16 + AVX512VL |
VFPCLASSPH k {k}, m128/m16bcst, imm8
VFPCLASSPH_MASKmskw_MASKmskw_MEMf16_IMM8_AVX512_VL128 | EVEX.LLZ.NP.0F3A.W0 66 /r ib | AVX10.1 or AVX512_FP16 + AVX512VL |
VFPCLASSPH k {k}, ymm, imm8
VFPCLASSPH_MASKmskw_MASKmskw_YMMf16_IMM8_AVX512 | EVEX.256.NP.0F3A.W0 66 /r ib | AVX10.1 or AVX512_FP16 + AVX512VL |
VFPCLASSPH k {k}, m256/m16bcst, imm8
VFPCLASSPH_MASKmskw_MASKmskw_MEMf16_IMM8_AVX512_VL256 | EVEX.LLZ.NP.0F3A.W0 66 /r ib | AVX10.1 or AVX512_FP16 + AVX512VL |
VFPCLASSPH k {k}, zmm, imm8
VFPCLASSPH_MASKmskw_MASKmskw_ZMMf16_IMM8_AVX512 | EVEX.512.NP.0F3A.W0 66 /r ib | AVX10.1 or AVX512_FP16 |
VFPCLASSPH k {k}, m512/m16bcst, imm8
VFPCLASSPH_MASKmskw_MASKmskw_MEMf16_IMM8_AVX512_VL512 | EVEX.LLZ.NP.0F3A.W0 66 /r ib | AVX10.1 or AVX512_FP16 |
Intrinsics
The C intrinsics of Clang 23.1.2 that compile to VFPCLASSPH, 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_fpclass_ph_mask
__mmask8 _mm_fpclass_ph_mask(__m128h A, const int imm) |
|
_mm_mask_fpclass_ph_mask
__mmask8 _mm_mask_fpclass_ph_mask(__mmask8 U, __m128h A, const int imm) |
|
_mm256_fpclass_ph_mask
__mmask16 _mm256_fpclass_ph_mask(__m256h A, const int imm) |
|
_mm256_mask_fpclass_ph_mask
__mmask16 _mm256_mask_fpclass_ph_mask(__mmask16 U, __m256h A, const int imm) |
|
_mm512_fpclass_ph_mask
__mmask32 _mm512_fpclass_ph_mask(__m512h A, const int imm) |
|
_mm512_mask_fpclass_ph_mask
__mmask32 _mm512_mask_fpclass_ph_mask(__mmask32 U, __m512h A, const int imm) |
|
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.
| ISA set | CPUID | Processors in XED |
|---|---|---|
AVX512_FP16_128 | AVX10.1 or AVX512_FP16 + AVX512VL | Nova Lake, Sapphire Rapids, Emerald Rapids, Granite Rapids, Diamond Rapids |
AVX512_FP16_256 | AVX10.1 or AVX512_FP16 + AVX512VL | Nova Lake, Sapphire Rapids, Emerald Rapids, Granite Rapids, Diamond Rapids |
AVX512_FP16_512 | AVX10.1 or AVX512_FP16 | Nova Lake, Sapphire Rapids, Emerald Rapids, Granite Rapids, Diamond Rapids |
More AVX10.1 instructions
- VFNMADD231SS
- VFNMSUB132PD
- VFNMSUB132PH
- VFNMSUB132PS
- VFNMSUB132SD
- VFNMSUB132SH
- VFNMSUB132SS
- VFNMSUB213PD
- VFNMSUB213PH
- VFNMSUB213PS
- VFNMSUB213SD
- VFNMSUB213SH
- VFNMSUB213SS
- VFNMSUB231PD
- VFNMSUB231PH
- VFNMSUB231PS
- VFNMSUB231SD
- VFNMSUB231SH
- VFNMSUB231SS
- VFPCLASSPD
- VFPCLASSPS
- VFPCLASSSD
- VFPCLASSSH
- VFPCLASSSS
- VGATHERDPD
- VGATHERDPS
- VGATHERQPD
- VGATHERQPS
- VGETEXPPD
- VGETEXPPH
- VGETEXPPS
- VGETEXPSD
- VGETEXPSH
- VGETEXPSS
- VGETMANTPD
- VGETMANTPH
- VGETMANTPS
- VGETMANTSD
- VGETMANTSH
- VGETMANTSS
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.