Extensions
Forms
6 (6 EVEX)
Data
Intel XED v2026.08.23

VCVT2PH2HF8S is VCVT2PH2HF8 with saturation: it converts the halves of two registers to E4M3 into one register, the third operand’s halves to the low half of the destination and the second operand’s to the high half, and gives 448, the largest E4M3 value, with the half’s sign wherever the plain form would give the NaN for a value too large: 7Eh for a half above 464 and FEh below -464. A NaN still gives 7Fh or FFh. Rounding is to nearest even whatever MXCSR says, denormal results are kept, and nothing is flagged. It is opcode 1Bh with the F2 prefix in EVEX map 5, takes a broadcast half and a write mask of up to 64 bits, and VCVTPH2HF8S is the one-source form.

Infinity

For an infinite half the AVX10.2 specification differs with itself, as VCVTPH2HF8S’s page explains: its description and helper function give 448 of the same sign, which the Operation block here follows, and its Table 3.6 gives the NaN.

In our builds

GCC 14 rejects -mavx10.2. Clang 23 compiles _mm512_cvts_2ph_hf8(a, b) to vcvt2ph2hf8s zmm0, zmm0, zmm1, so a fills the high half; _mm256_ and _mm_ forms exist. No AVX10.2 processor appears in this site’s recorded cases.

Forms

Every encoding of VCVT2PH2HF8S that Intel XED knows, one row per XED instruction form (iform). How to read the notation.
InstructionEncodingRequires
VCVT2PH2HF8S xmm {k}{z}, xmm, xmm VCVT2PH2HF8S_XMMhf8_MASKmskw_XMMf16_XMMf16_AVX512EVEX.128.F2.MAP5.W0 1B /rAVX10.2 or AVX10_V1_AUX
VCVT2PH2HF8S xmm {k}{z}, xmm, m128/m16bcst VCVT2PH2HF8S_XMMhf8_MASKmskw_XMMf16_MEMf16_AVX512EVEX.128.F2.MAP5.W0 1B /rAVX10.2 or AVX10_V1_AUX
VCVT2PH2HF8S ymm {k}{z}, ymm, ymm VCVT2PH2HF8S_YMMhf8_MASKmskw_YMMf16_YMMf16_AVX512EVEX.256.F2.MAP5.W0 1B /rAVX10.2 or AVX10_V1_AUX
VCVT2PH2HF8S ymm {k}{z}, ymm, m256/m16bcst VCVT2PH2HF8S_YMMhf8_MASKmskw_YMMf16_MEMf16_AVX512EVEX.256.F2.MAP5.W0 1B /rAVX10.2 or AVX10_V1_AUX
VCVT2PH2HF8S zmm {k}{z}, zmm, zmm VCVT2PH2HF8S_ZMMhf8_MASKmskw_ZMMf16_ZMMf16_AVX512EVEX.512.F2.MAP5.W0 1B /rAVX10.2 or AVX10_V1_AUX
VCVT2PH2HF8S zmm {k}{z}, zmm, m512/m16bcst VCVT2PH2HF8S_ZMMhf8_MASKmskw_ZMMf16_MEMf16_AVX512EVEX.512.F2.MAP5.W0 1B /rAVX10.2 or AVX10_V1_AUX

Data flow

Where the elements of the sources go, element 0 on the right; results that depend on a control value are drawn for an example. How to read.

Two sources narrowed into one: the halves of xmm3 fill the low half of the result, those of xmm2 the high half.
VCVT2PH2HF8S: two sources narrowed into oneResult bytes 15 to 0: a7, unchanged (bit 14 of k1 is 0), a5, a4, a3, a2, a1, a0, b7, b6, b5, b4, b3, b2, b1, b0.01234567xmm2a1111111111111110k1b0b1b2b3b4b5b6b7a0a1a2a3a4a5a7xmm101234567xmm3or m128b

Shown for the xmm form; the ymm and zmm forms work the same on 32 and 64 halves. The forms write under a mask: where its bit is 0, the element keeps its old value, or zeroes it with {z}. With m16bcst, one half from memory stands for every element of xmm3.

Result bytes 15 to 0: a7, unchanged (bit 14 of k1 is 0), a5, a4, a3, a2, a1, a0, b7, b6, b5, b4, b3, b2, b1, b0.

Operation

What the forms do, in pseudocode that our tests run against results recorded on real processors. How to read.

for i in range(VL // 8):
    if k1[i]:
        if i < VL // 16:
            x = src3.f16[i]
        else:
            x = zmm2.f16[i - VL // 16]
        zmm1.hf8[i] = to_hf8s(x)
    elif zeroing:
        zmm1.hf8[i] = 0
    # else: zmm1.hf8[i] keeps its value
# m16bcst: src3.f16[i] is the m16 for every i
# HF8: to nearest even, denormals kept, no flags; MXCSR unused
# zmm1 is zeroed from bit VL up

Not run on a processor: none of these processors has AVX10.2. The tests check its arithmetic against MPFR.

Operands

What each form reads and writes, as Intel XED records it: the operands of its syntax, in order, and the implicit ones that the syntax does not name. How to read.
OperandKindAction
VCVT2PH2HF8S xmm {k}{z}, xmm, xmm/m128/m16bcst VCVT2PH2HF8S ymm {k}{z}, ymm, ymm/m256/m16bcst VCVT2PH2HF8S zmm {k}{z}, zmm, zmm/m512/m16bcst
xmm, ymm, zmmexplicitwrite (masked)
{k}explicitread (write mask)
xmm, ymm, zmmexplicitread
xmm/m128/m16bcst, ymm/m256/m16bcst, zmm/m512/m16bcstexplicitread

Flags

None: XED records no flag that the forms test or change.

Exceptions

The exception class is XED's name for the set of exception conditions that a form follows. How to read.

All forms
AVX512-E4NF

Attributes

What else XED records about the forms. How to read.

All forms
write masking; always rounds to nearest even
Memory forms
embedded broadcast (tuple Full)

Intrinsics

The C intrinsics of Clang 23.1.2 that compile to VCVT2PH2HF8S, 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.

IntrinsicCompiles to
_mm_cvts_2ph_hf8 __m128i _mm_cvts_2ph_hf8(__m128h __A, __m128h __B)

VCVT2PH2HF8S xmm, xmm, xmm EVEX.128 -mavx10.2

_mm_mask_cvts_2ph_hf8 __m128i _mm_mask_cvts_2ph_hf8(__m128i __W, __mmask16 __U, __m128h __A, __m128h __B)

VCVT2PH2HF8S xmm {k}, xmm, xmm EVEX.128 -mavx10.2

_mm_maskz_cvts_2ph_hf8 __m128i _mm_maskz_cvts_2ph_hf8(__mmask16 __U, __m128h __A, __m128h __B)

VCVT2PH2HF8S xmm {k}{z}, xmm, xmm EVEX.128 -mavx10.2

_mm256_cvts_2ph_hf8 __m256i _mm256_cvts_2ph_hf8(__m256h __A, __m256h __B)

VCVT2PH2HF8S ymm, ymm, ymm EVEX.256 -mavx10.2

_mm256_mask_cvts_2ph_hf8 __m256i _mm256_mask_cvts_2ph_hf8(__m256i __W, __mmask32 __U, __m256h __A, __m256h __B)

VCVT2PH2HF8S ymm {k}, ymm, ymm EVEX.256 -mavx10.2

_mm256_maskz_cvts_2ph_hf8 __m256i _mm256_maskz_cvts_2ph_hf8(__mmask32 __U, __m256h __A, __m256h __B)

VCVT2PH2HF8S ymm {k}{z}, ymm, ymm EVEX.256 -mavx10.2

_mm512_cvts_2ph_hf8 __m512i _mm512_cvts_2ph_hf8(__m512h __A, __m512h __B)

VCVT2PH2HF8S zmm, zmm, zmm EVEX.512 -mavx10.2

_mm512_mask_cvts_2ph_hf8 __m512i _mm512_mask_cvts_2ph_hf8(__m512i __W, __mmask64 __U, __m512h __A, __m512h __B)

VCVT2PH2HF8S zmm {k}, zmm, zmm EVEX.512 -mavx10.2

_mm512_maskz_cvts_2ph_hf8 __m512i _mm512_maskz_cvts_2ph_hf8(__mmask64 __U, __m512h __A, __m512h __B)

VCVT2PH2HF8S zmm {k}{z}, zmm, zmm EVEX.512 -mavx10.2

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.

CPUID requirements and processors of the XED ISA sets above. Alternatives are separated by “or”; processors follow XED’s chip model, whose AMD processors end with Zen 2, and the CPU data of this site for Zen 3 to Zen 6.
ISA setCPUIDProcessors
AVX512_FP8_CONVERT_128

AVX10.2
CPUID.(EAX=07H,ECX=1):EDX[19] AVX10
CPUID.(EAX=24H,ECX=0):EBX[7:0] ≥ 2 AVX10 version

or

AVX10_V1_AUX
CPUID.(EAX=24H,ECX=1):ECX[2] AVX10_V1_AUX

Nova Lake, Diamond Rapids
AVX512_FP8_CONVERT_256
Same as AVX512_FP8_CONVERT_128Same as AVX512_FP8_CONVERT_128
AVX512_FP8_CONVERT_512
Same as AVX512_FP8_CONVERT_128Same as AVX512_FP8_CONVERT_128

More AVX10.2 instructions

All 96 AVX10.2 instructions

Sources

  1. Intel XED v2026.08.23 (commit 0bcb6237345c): forms, encodings, operands, flags, exception classes, attributes, ISA sets, CPUID bits and chip model.
  2. 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.
  3. Intel Advanced Vector Extensions 10.2 Architecture Specification, revision 7.0 (361050-007, April 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.