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

TCVTROWPS2BF16L moves one row of singles from a tile into a ZMM register and rounds each to bfloat16, as TCVTROWPS2BF16H does, but puts the result in the low half of its dword and zeros the high half. That page covers the rounding, always to nearest even, and the treatment of denormals and NaNs; TILEMOVROW’s covers the row number and the faults.

Same conversion, different place

Each result is the H form’s result shifted right by 16 bits: 1 + 2^-8 as a single gives 00003F80H, and an out-of-range row or an element past the row’s width gives a zero dword in either form. The low half is the even-numbered word of a dword, and it is also where the even-numbered elements of a bfloat16 pair sit. In a TDPBF16PS source, the lower row of two interleaved rows of B goes there, so this instruction converts that row and the H form its neighbour.

Used alone, the L form leaves each number in the low 16 bits of a dword with zeros above it, which is what a later word-level narrowing such as VPMOVDW needs: it packs 16 dwords’ low words into a YMM register, the layout VCVTNEPS2BF16 gives directly from a ZMM register.

Two opcodes

The register form is EVEX opcode 6Dh of map 0F38 with the F3 prefix bits, one prefix away from the H form’s F2. The immediate form has opcode 77h of map 0F3A with F3, where the H form has 07h with F2: tcvtrowps2bf16l zmm1, tmm2, 1 is 62 F3 7E 48 77 CA 01.

In our builds

GCC 14 has no -mamx-avx512 option. With it and -mavx512bf16, Clang 23 at -O2 compiles _tile_cvtrowps2bf16l(2, 1) with a constant row through a register, mov eax, 1 and tcvtrowps2bf16l zmm0, tmm2, eax; _tile_cvtrowps2bf16li(2, 1) gives the immediate form. Zen 5 has no AMX, and this site’s recorded cases include none of TCVTROWPS2BF16L.

Forms

Every encoding of TCVTROWPS2BF16L that Intel XED knows, one row per XED instruction form (iform). How to read the notation.
InstructionEncodingRequires
TCVTROWPS2BF16L zmm, tmm, r32 64-bit mode only TCVTROWPS2BF16L_ZMMbf16_TMMf32_GPR32u32EVEX.512.F3.0F38.W0 6D /rACE v1 or AMX_AVX512
TCVTROWPS2BF16L zmm, tmm, imm8 64-bit mode only TCVTROWPS2BF16L_ZMMbf16_TMMf32_IMM8EVEX.512.F3.0F3A.W0 77 /r ibACE v1 or AMX_AVX512

Operation

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

on = xcr0 if cr4 >> 18 & 1 else 0    # XCR0, where CR4.OSXSAVE is set
if on >> 17 & 3 != 3:                # TILECFG and TILEDATA
    fault(UD)
if on & 0xE6 != 0xE6:                # AVX-512's state, AVX's and
    fault(UD)                        # SSE's
if palette == 0 or not tmm2.rows:    # no configuration, or a tile it
    fault(UD)                        # leaves out
if tmm2.colsb % 4:                   # whole dwords
    fault(UD)
if cr0 >> 3 & 1 or xfd >> 18 & 1:    # CR0.TS, or the OS keeps the
    fault(NM)                        # tiles from this thread
# ACE's exception class for these forms asks for XCR0 bit 20
# (SCALEDATA) too
r = src3 & 15                        # bits 3:0 of imm8 or r32
x = tmm2.row[r]
n = tmm2.colsb // 4 if r < tmm2.rows else 0
for i in range(16):
    if i < n:
        v = to_bf16_ne(x.f32[i])
        zmm1.d[i] = v                # the high half 0
    else:                            # past the tile's rows or colsb
        zmm1.d[i] = 0
start_row = 0

Not run on a processor: none of these processors has AMX.

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
TCVTROWPS2BF16L zmm, tmm, r32 64-bit mode only
zmmexplicitwrite
tmmexplicitread
r32explicitread
TCVTROWPS2BF16L zmm, tmm, imm8 64-bit mode only
zmmexplicitwrite
tmmexplicitread
imm8explicitread

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.

TCVTROWPS2BF16L zmm, tmm, r32 64-bit mode only
AMX-E8-EVEX
TCVTROWPS2BF16L zmm, tmm, imm8 64-bit mode only
AMX-E7-EVEX

Attributes

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

All forms
may abort a TSX transaction

Intrinsics

The C intrinsics of Clang 23.1.2 that compile to TCVTROWPS2BF16L, 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
_tile_cvtrowps2bf16l __m512bh _tile_cvtrowps2bf16l(const int tsrc, const int row)

TCVTROWPS2BF16L zmm, tmm, r32 EVEX.512 -mamx-avx512 -mavx10.2

_tile_cvtrowps2bf16li __m512bh _tile_cvtrowps2bf16li(const int tsrc, const int imm8)

TCVTROWPS2BF16L zmm, tmm, imm8 EVEX.512 -mamx-avx512 -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
AMX_AVX512

ACE v1
CPUID.(EAX=07H,ECX=1):ECX[11] ACE
CPUID.(EAX=1DH,ECX=2):EAX[7:0] ≥ 1 ACE version

or

AMX_AVX512
CPUID.(EAX=1EH,ECX=1):EAX[7] AMX_AVX512

Diamond Rapids

More AMX-AVX512 instructions

More ACE 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 Architecture Instruction Set Extensions and Future Features Programming Reference (319433-062, June 2026): page 3-17 (TCVTROWPS2BF16[H,L])
  4. x86 Ecosystem Advisory Group: AI Compute Extensions (ACE) Specification, version 1.16.2 (July 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.