Instruction
VCVT2PH2HF8S
Converts two vectors of half-precision values into one vector of E4M3 FP8 values, saturating values too large for FP8 to its largest normal.
- 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
| Instruction | Encoding | Requires |
|---|---|---|
VCVT2PH2HF8S xmm {k}{z}, xmm, xmm
VCVT2PH2HF8S_XMMhf8_MASKmskw_XMMf16_XMMf16_AVX512 | EVEX.128.F2.MAP5.W0 1B /r | AVX10.2 or AVX10_V1_AUX |
VCVT2PH2HF8S xmm {k}{z}, xmm, m128/m16bcst
VCVT2PH2HF8S_XMMhf8_MASKmskw_XMMf16_MEMf16_AVX512 | EVEX.128.F2.MAP5.W0 1B /r | AVX10.2 or AVX10_V1_AUX |
VCVT2PH2HF8S ymm {k}{z}, ymm, ymm
VCVT2PH2HF8S_YMMhf8_MASKmskw_YMMf16_YMMf16_AVX512 | EVEX.256.F2.MAP5.W0 1B /r | AVX10.2 or AVX10_V1_AUX |
VCVT2PH2HF8S ymm {k}{z}, ymm, m256/m16bcst
VCVT2PH2HF8S_YMMhf8_MASKmskw_YMMf16_MEMf16_AVX512 | EVEX.256.F2.MAP5.W0 1B /r | AVX10.2 or AVX10_V1_AUX |
VCVT2PH2HF8S zmm {k}{z}, zmm, zmm
VCVT2PH2HF8S_ZMMhf8_MASKmskw_ZMMf16_ZMMf16_AVX512 | EVEX.512.F2.MAP5.W0 1B /r | AVX10.2 or AVX10_V1_AUX |
VCVT2PH2HF8S zmm {k}{z}, zmm, m512/m16bcst
VCVT2PH2HF8S_ZMMhf8_MASKmskw_ZMMf16_MEMf16_AVX512 | EVEX.512.F2.MAP5.W0 1B /r | AVX10.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.
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 upNot run on a processor: none of these processors has AVX10.2. The tests check its arithmetic against MPFR.
Operands
| Operand | Kind | Action |
|---|---|---|
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, zmm | explicit | write (masked) |
{k} | explicit | read (write mask) |
xmm, ymm, zmm | explicit | read |
xmm/m128/m16bcst, ymm/m256/m16bcst, zmm/m512/m16bcst | explicit | read |
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.
| Intrinsic | Compiles to |
|---|---|
_mm_cvts_2ph_hf8
__m128i _mm_cvts_2ph_hf8(__m128h __A, __m128h __B) |
|
_mm_mask_cvts_2ph_hf8
__m128i _mm_mask_cvts_2ph_hf8(__m128i __W, __mmask16 __U, __m128h __A, __m128h __B) |
|
_mm_maskz_cvts_2ph_hf8
__m128i _mm_maskz_cvts_2ph_hf8(__mmask16 __U, __m128h __A, __m128h __B) |
|
_mm256_cvts_2ph_hf8
__m256i _mm256_cvts_2ph_hf8(__m256h __A, __m256h __B) |
|
_mm256_mask_cvts_2ph_hf8
__m256i _mm256_mask_cvts_2ph_hf8(__m256i __W, __mmask32 __U, __m256h __A, __m256h __B) |
|
_mm256_maskz_cvts_2ph_hf8
__m256i _mm256_maskz_cvts_2ph_hf8(__mmask32 __U, __m256h __A, __m256h __B) |
|
_mm512_cvts_2ph_hf8
__m512i _mm512_cvts_2ph_hf8(__m512h __A, __m512h __B) |
|
_mm512_mask_cvts_2ph_hf8
__m512i _mm512_mask_cvts_2ph_hf8(__m512i __W, __mmask64 __U, __m512h __A, __m512h __B) |
|
_mm512_maskz_cvts_2ph_hf8
__m512i _mm512_maskz_cvts_2ph_hf8(__mmask64 __U, __m512h __A, __m512h __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.
| ISA set | CPUID | Processors |
|---|---|---|
AVX512_FP8_CONVERT_128 | AVX10.2 or AVX10_V1_AUX | Nova Lake, Diamond Rapids |
AVX512_FP8_CONVERT_256 | Same as AVX512_FP8_CONVERT_128 | Same as AVX512_FP8_CONVERT_128 |
AVX512_FP8_CONVERT_512 | Same as AVX512_FP8_CONVERT_128 | Same as AVX512_FP8_CONVERT_128 |
More AVX10.2 instructions
- VADDBF16
- VCMPBF16
- VCOMISBF16
- VCOMXSD
- VCOMXSH
- VCOMXSS
- VCVT2PH2BF8
- VCVT2PH2BF8S
- VCVT2PH2HF8
- VCVT2PS2PHX
- VCVTBF162IBS
- VCVTBF162IUBS
- VCVTBIASPH2BF8
- VCVTBIASPH2BF8S
- VCVTBIASPH2HF8
- VCVTBIASPH2HF8S
- VCVTHF82PH
- VCVTPH2BF8
- VCVTPH2BF8S
- VCVTPH2HF8
- VCVTPH2HF8S
- VCVTPH2IBS
- VCVTPH2IUBS
- VCVTPS2IBS
- VCVTPS2IUBS
- VCVTTBF162IBS
- VCVTTBF162IUBS
- VCVTTPD2DQS
- VCVTTPD2QQS
- VCVTTPD2UDQS
- VCVTTPD2UQQS
- VCVTTPH2IBS
- VCVTTPH2IUBS
- VCVTTPS2DQS
- VCVTTPS2IBS
- VCVTTPS2IUBS
- VCVTTPS2QQS
- VCVTTPS2UDQS
- VCVTTPS2UQQS
- VCVTTSD2SIS
Sources
- Intel XED v2026.08.23 (commit
0bcb6237345c): forms, encodings, operands, flags, exception classes, attributes, 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 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.