Instruction
VSCATTERDPS
Stores singles to memory at addresses formed with a vector of 32-bit indices, for the elements a mask selects.
- Extensions
- Forms
- 3 (3 EVEX)
- Data
- Intel XED v2026.08.23
VSCATTERDPS stores the singles of a vector to scattered addresses: element i goes to a base plus element i of a vector of signed 32-bit indices, times 1, 2, 4 or 8. It is the store that mirrors VGATHERDPS, and it works exactly as VPSCATTERDD, whose page covers the mask that is cleared as elements are stored, repeated indices and the cost of a scatter: the singles are moved as 32-bit patterns, so nothing is rounded and no MXCSR flag is raised. Like every scatter it exists only in AVX-512, and K0, which would mean no mask, is not allowed.
Signed indices
The indices are sign-extended before the scaling, so they reach below
the base as well as above it. In a case recorded on Zen 5,
vscatterdps [base + zmm14*4]{k5}, zmm7 stored eleven of its 16
elements, those K5 selected, at indices from -15 to 14, element 14
with index -15 going to 60 bytes below the base; the other 21 dwords
of the buffer kept their values, and K5 ended as zero. The XMM and YMM
forms, which take 4 and 8 indices, did the same with their low mask
bits.
In compiled code
GCC 14 and Clang 23 at -O2 vectorize d[idx[i]] = s[i] over float
for -march=x86-64-v4: GCC with ZMM registers and an all-ones mask
from KXNORW, Clang with YMM registers and
KXNORB. Clang also scatters where the addresses
follow a constant stride: d[5*i] = s[i] became
VSCATTERQPS with a vector of constant 64-bit
offsets, while GCC kept that loop scalar.
Intel’s optimization manual uses VSCATTERDPS in its scatter example
(Section 17.11.1): dst[ind[i]] = (float)src[i] with 64-bit integer
sources, where the hardware version converts two ZMM registers with
VCVTUQQ2PS, joins the halves with VSHUFF32X4 and
stores the 16 results with one VSCATTERDPS under a mask made by KXNORW.
With int64_t sources and -march=x86-64-v4, our builds of that loop
scatter as well: GCC converts two ZMM registers with
VCVTQQ2PS, joins them with VINSERTF32X8 and
scatters 16 singles at once, much as Intel’s example does, while Clang
converts and scatters four at a time in XMM registers.
In the optimization guide
What the optimization guide says about VSCATTERDPS, a line per claim. Each links to the claim in the guide, with its sources and where they differ.
Vectors
- Gathers and scatters: Scatters store one element at a time; Intel replaces short-stride scatters by permutes and stores, and they are microcode on Zen 5.
Forms
| Instruction | Encoding | Requires |
|---|---|---|
VSCATTERDPS vm32z {k}, zmm
VSCATTERDPS_MEMf32_MASKmskw_ZMMf32_AVX512_VL512 | EVEX.512.66.0F38.W0 A2 /r | AVX10.1 or AVX512F |
VSCATTERDPS vm32x {k}, xmm
VSCATTERDPS_MEMf32_MASKmskw_XMMf32_AVX512_VL128 | EVEX.128.66.0F38.W0 A2 /r | AVX10.1 or AVX512F + AVX512VL |
VSCATTERDPS vm32y {k}, ymm
VSCATTERDPS_MEMf32_MASKmskw_YMMf32_AVX512_VL256 | EVEX.256.66.0F38.W0 A2 /r | AVX10.1 or AVX512F + AVX512VL |
Latency and throughput
| Model | vm32z {k}, zmm | vm32x {k}, xmm | vm32y {k}, ymm |
|---|---|---|---|
| Skylake-SP | 7 / 16p0156 | 8 / 4p0156 | 8 / 8p0156 |
| Ice Lake | 7 / 8p0156 | 8 / 2p0156 | 8 / 4p0156 |
| Sapphire Rapids | 19 / 8p0 p1 p5 p6 p11 | 12 / 2p0 p1 p5 p6 p11 | 12 / 4p0 p1 p5 p6 p11 |
| Zen 4 | 1 / 1AGU0 AGU1 AGU2 LSU Store | 1 / 1AGU0 AGU1 AGU2 LSU Store | 1 / 1AGU0 AGU1 AGU2 LSU Store |
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.
Example: indices 3, 14, 0, 7, 5, 11, 2, 5 from element 7 down, mask k1 = 0xFB; memory elements are numbered from the base address in units of the scale. The other forms scatter 4 and 16 elements, one for each index. The mask is cleared as the elements complete.
With the example indices, memory elements 15 to 0: unchanged, a6, unchanged, unchanged, unchanged, unchanged, unchanged, unchanged, a4, unchanged, a3, unchanged, a7, a1, unchanged, a5.
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 // 32):
if k1[i]:
a = mem.index.sd[i] * mem.scale
store(mem.base + a, 32, zmm2.d[i])
k1.write(0) # all of it
Run on AMD Zen 5 (EPYC 9645): 3 cases.
Operands
| Operand | Kind | Action |
|---|---|---|
VSCATTERDPS vm32x {k}, xmm VSCATTERDPS vm32y {k}, ymm VSCATTERDPS vm32z {k}, zmm | ||
vm32x, vm32y, vm32z | explicit | write (masked) |
{k} | explicit | read, write (write mask) |
xmm, ymm, zmm | 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-E12
Attributes
What else XED records about the forms. How to read.
- All forms
- scatter; write masking; memory fault suppression
Intrinsics
The C intrinsics of Clang 23.1.2 that compile to VSCATTERDPS, 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_i32scatter_ps
void _mm_i32scatter_ps(void *addr, __m128i index, __m128 v1, const int scale) |
|
_mm_mask_i32scatter_ps
void _mm_mask_i32scatter_ps(void *addr, __mmask8 mask, __m128i index, __m128 v1, const int scale) |
|
_mm256_i32scatter_ps
void _mm256_i32scatter_ps(void *addr, __m256i index, __m256 v1, const int scale) |
|
_mm256_mask_i32scatter_ps
void _mm256_mask_i32scatter_ps(void *addr, __mmask8 mask, __m256i index, __m256 v1, const int scale) |
|
_mm512_i32scatter_ps
void _mm512_i32scatter_ps(void *addr, __m512i index, __m512 v1, const int scale) |
|
_mm512_mask_i32scatter_ps
void _mm512_mask_i32scatter_ps(void *addr, __mmask16 mask, __m512i index, __m512 v1, const int scale) |
|
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 |
|---|---|---|
AVX512F_512 | AVX10.1 or AVX512F | Cannon Lake, Ice Lake (client), Tiger Lake, Nova Lake, Skylake-SP, Cascade Lake, Cooper Lake, Ice Lake (server), Sapphire Rapids, Emerald Rapids, Granite Rapids, Diamond Rapids, Knights Landing, Knights Mill, Zen 4, Zen 5, Zen 6 |
AVX512F_128 | AVX10.1 or AVX512F + AVX512VL | Cannon Lake, Ice Lake (client), Tiger Lake, Nova Lake, Skylake-SP, Cascade Lake, Cooper Lake, Ice Lake (server), Sapphire Rapids, Emerald Rapids, Granite Rapids, Diamond Rapids, Zen 4, Zen 5, Zen 6 |
AVX512F_256 | Same as AVX512F_128 | Same as AVX512F_128 |
More AVX10.1 instructions
- VREDUCESS
- VRNDSCALEPD
- VRNDSCALEPH
- VRNDSCALEPS
- VRNDSCALESD
- VRNDSCALESH
- VRNDSCALESS
- VRSQRT14PD
- VRSQRT14PS
- VRSQRT14SD
- VRSQRT14SS
- VRSQRTPH
- VRSQRTSH
- VSCALEFPD
- VSCALEFPH
- VSCALEFPS
- VSCALEFSD
- VSCALEFSH
- VSCALEFSS
- VSCATTERDPD
- VSCATTERQPD
- VSCATTERQPS
- VSHUFF32X4
- VSHUFF64X2
- VSHUFI32X4
- VSHUFI64X2
- VSHUFPD
- VSHUFPS
- VSQRTPD
- VSQRTPH
- VSQRTPS
- VSQRTSD
- VSQRTSH
- VSQRTSS
- VSUBPD
- VSUBPH
- VSUBPS
- VSUBSD
- VSUBSH
- VSUBSS
Sources
- Intel XED v2026.08.23 (commit
0bcb6237345c): forms, encodings, operands, flags, exception classes, attributes, ISA sets, CPUID bits and chip model. - The CPU data of x86-64.net: Zen 3 to Zen 6, from GCC’s
-marchfeature sets and AMD’s Processor Programming References, which the page of each processor cites. - 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. - LLVM 23.1.2's x86 scheduling models (commit
85ac56026243): the latency, reciprocal throughput and ports of each form, as llvm-mca reports them. - Intel Advanced Vector Extensions 10.2 Architecture Specification, revision 7.0 (361050-007, April 2026)
- Intel 64 and IA-32 Architectures Software Developer's Manual, Volume 2 (325383-093, September 2026): Volume 2C, page 5-740 (VSCATTERDPS/
VSCATTERDPD/ VSCATTERQPS/ VSCATTERQPD) - Intel 64 and IA-32 Architectures Optimization Reference Manual, Volume 1 (248966-051, October 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 and the timings from LLVM's scheduling models, both part of the LLVM Project, licensed under the Apache License 2.0 with LLVM Exceptions. The text is our own.