Instruction
VPGATHERQQ
Loads quadwords from memory at addresses formed with a vector of 64-bit indices, for the elements a mask selects.
VPGATHERQQ loads quadwords from scattered addresses, each a base plus a signed 64-bit index times a scale of 1, 2, 4 or 8. It works like VGATHERDPS, whose page explains the mask that selects the elements and is cleared as they load, the register rules that raise #UD, and why compiled code rebuilds the mask before each gather. What sets VPGATHERQQ apart is that the index and the data have the same width: 4 indices in a ymm register fetch 4 quadwords, and 8 in a zmm register fetch 8, so both registers are full. A 32-bit index fetching quadwords, VPGATHERDQ, needs only half a register of indices; a 64-bit index fetching doublewords, VPGATHERQD, fills only half of its destination.
Pointers as indices
A 64-bit index can hold a whole address. For d[i] = *p[i], an array of
pointers, Clang 23 at -O2 gathers with no base register and a scale of
1, vpgatherqq zmm4 {k1}, qword ptr [1*zmm0], which follows eight
pointers at once; with a table, d[i] = t[idx[i]] over int64_t
indices becomes [rdx + 8*zmm0]. Clang does this on zmm registers for
-march=znver4 and znver5 and on ymm for x86-64-v4,
skylake-avx512 and icelake-server, and keeps both loops scalar for
x86-64-v3, where the VEX form exists. GCC 14 vectorized neither loop
for any of these targets. Each element’s address needs no alignment.
Cost
AMD’s Zen 5 guide lists VPGATHERQQ as microcoded, like every gather, and advises vector loads and shuffles instead when the indices are known in advance (Section 2.11.2). Intel’s optimization guide lists the access patterns that suit loads and shuffles better, sequential elements, fewer than four of them, small strides and transpositions, and those that suit a gather, such as indices computed in vector registers or loads that depend on a condition per element (Section 15.16.4, Examples 15-43 and 15-44). It also notes that the latency of a 256-bit gather is less than twice that of a 128-bit one, so wider gathers pay off better.
VPSCATTERQQ stores quadwords the same way, and VGATHERQPD loads doubles with 64-bit indices.
In the optimization guide
What the optimization guide says about VPGATHERQQ, a line per claim. Each links to the claim in the guide, with its sources and where they differ.
Vectors
- Gathers and scatters: Where the layout of the data is known, vector loads and shuffles usually beat a gather.
- Gathers and scatters: Gathers beat scalar loads on Skylake, while AMD lists them as microcode on Zen 3, Zen 4 and Zen 5.
Crestmont and Gracemont
- Vectors and AVX2: Gathers are microcoded on these cores and take about 50 cycles.
Golden Cove and Raptor Cove
- Vectors, AVX-512 and AMX: A gather is a load micro-op for each element plus a few more: LLVM’s models give an eight-element VPGATHERDD 12 micro-ops and a latency of 30 cycles, and the 16-element one of Sapphire Rapids 19 micro-ops.
Haswell and Broadwell
- Gathers: Haswell is the first core with gathers, and each one runs as many micro-ops; Broadwell runs them much faster.
Skylake to Cooper Lake
- Vectors on all parts: Gathers are faster than on Broadwell and beat a sequence of scalar loads unless they fetch only two elements or the data comes from memory rather than the caches.
Zen 2
- Vectors and floating point: Gathers such as VPGATHERDD are microcoded, in AMD’s spreadsheet and LLVM’s model, so vector loads and shuffles beat them when the indices are known in advance.
Zen 3
- Vectors and floating point: Gathers such as VPGATHERDD are microcoded, and a register loaded in pieces is slower than one full-width load, so vector loads and shuffles beat both when the indices are known in advance.
Zen 4
- Vectors and floating point: A gather is slower than vector loads and shuffles when the indices are known in advance, and a register loaded in pieces is slower than one full-width load.
Zen 5
- Vectors and floating point: A gather is slower than vector loads and shuffles when the indices are known in advance.
Forms
| Instruction | Encoding | Requires |
|---|---|---|
VPGATHERQQ ymm, vm64y, ymm
VPGATHERQQ_YMMu64_MEMq_YMMi64_VL256 | VEX.256.66.0F38.W1 91 /r | AVX2 |
VPGATHERQQ xmm, vm64x, xmm
VPGATHERQQ_XMMu64_MEMq_XMMi64_VL128 | VEX.128.66.0F38.W1 91 /r | AVX2 |
VPGATHERQQ zmm {k}, vm64z
VPGATHERQQ_ZMMu64_MASKmskw_MEMu64_AVX512_VL512 | EVEX.512.66.0F38.W1 91 /r | AVX10.1 or AVX512F |
VPGATHERQQ xmm {k}, vm64x
VPGATHERQQ_XMMu64_MASKmskw_MEMu64_AVX512_VL128 | EVEX.128.66.0F38.W1 91 /r | AVX10.1 or AVX512F + AVX512VL |
VPGATHERQQ ymm {k}, vm64y
VPGATHERQQ_YMMu64_MASKmskw_MEMu64_AVX512_VL256 | EVEX.256.66.0F38.W1 91 /r | AVX10.1 or AVX512F + AVX512VL |
Latency and throughput
| Model | ymm, vm64y, ymm | xmm, vm64x, xmm | zmm {k}, vm64z | xmm {k}, vm64x | ymm {k}, vm64y |
|---|---|---|---|---|---|
| Haswell | 17 / 5p0156 | 15 / 3.33p0156 | |||
| Broadwell | 18 / 3p0156 | 17 / 3p0156 | |||
| Skylake | 20 / 2p015 | 18 / 1p015 | |||
| Skylake-SP, Ice Lake | 20 / 2p015 | 18 / 1p015 | 21 / 4p0156 | 17 / 1p0156 | 19 / 2p0156 |
| Alder Lake | 29 / 1.33p015 | 20 / 1p015 | |||
| Sapphire Rapids | 29 / 1.33p015 | 20 / 1p015 | 28 / 2.67p05 | 20 / 1p015 | 28 / 1.33p015 |
| Lunar Lake | 29 / 1.33V0 V1 V2 V3 p1 p3 p5 | 20 / 0.67V0 V1 V2 V3 p1 p3 p5 | |||
| Zen, Zen 2 | 100 / 0.25 | 100 / 0.25 | |||
| Zen 3 | 5 / 0.33AGU0 AGU1 AGU2 LSU Load | 5 / 0.33AGU0 AGU1 AGU2 LSU Load | |||
| Zen 4 | 5 / 0.33AGU0 AGU1 AGU2 LSU Load | 5 / 0.33AGU0 AGU1 AGU2 LSU Load | 5 / 0.33AGU0 AGU1 AGU2 LSU Load | 5 / 0.33AGU0 AGU1 AGU2 LSU Load | 5 / 0.33AGU0 AGU1 AGU2 LSU Load |
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 0, 11, 2, 5 from element 3 down, mask ymm3 = 0x0F; memory elements are numbered from the base address in units of the scale. The other forms gather 2 elements, one for each index. The AVX2 forms take the mask from the sign bits of a vector register; the mask is cleared as the elements complete.
With the example indices (m followed by the memory element), result quadwords 3 to 0: m0, m11, m2, m5.
Example: indices 3, 14, 7, 7, 0, 11, 2, 5 from element 7 down, mask k1 = 0xDF; memory elements are numbered from the base address in units of the scale. The other forms gather 2 and 4 elements, one for each index. The mask is cleared as the elements complete.
With the example indices (m followed by the memory element), result quadwords 7 to 0: m3, m14, unchanged, m7, m0, m11, m2, m5.
Operation
What the forms do, in pseudocode that our tests run against results recorded on real processors. How to read.
x = mem.index.number
if x in (ymm1.number, ymm3.number):
fault(UD)
if ymm1.number == ymm3.number:
fault(UD)
for i in range(VL // 64):
if ymm3.sq[i] < 0:
a = mem.index.sq[i] * mem.scale
ymm1.q[i] = load(mem.base + a, 64)
ymm3.write(0)
# ymm1 is zeroed from bit VL upRun on AMD Zen 5 (EPYC 9645): 2 cases.
if mem.index.number == zmm1.number:
fault(UD)
for i in range(VL // 64):
if k1[i]:
a = mem.index.sq[i] * mem.scale
zmm1.q[i] = load(mem.base + a, 64)
k1.write(0) # all of it
# zmm1 is zeroed from bit VL upRun on AMD Zen 5 (EPYC 9645): 3 cases.
Operands
| Operand | Kind | Action |
|---|---|---|
VPGATHERQQ xmm, vm64x, xmm VPGATHERQQ ymm, vm64y, ymm | ||
xmm, ymm | explicit | conditional read, write |
vm64x, vm64y | explicit | read |
xmm, ymm | explicit | read, write |
VPGATHERQQ xmm {k}, vm64x VPGATHERQQ ymm {k}, vm64y VPGATHERQQ zmm {k}, vm64z | ||
xmm, ymm, zmm | explicit | write (masked) |
{k} | explicit | read, write (write mask) |
vm64x, vm64y, vm64z | 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.
- VEX forms
avx-type-12- EVEX forms
AVX512-E12
Attributes
What else XED records about the forms. How to read.
- All forms
- gather
- EVEX forms
- write masking; memory fault suppression
Intrinsics
The C intrinsics of Clang 23.1.2 that compile to VPGATHERQQ, 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_i64gather_epi64
__m128i _mm_i64gather_epi64(long long const *m, __m128i i, const int s) |
|
_mm_mask_i64gather_epi64
__m128i _mm_mask_i64gather_epi64(__m128i a, long long const *m, __m128i i, __m128i mask, const int s) |
|
_mm_mmask_i64gather_epi64
__m128i _mm_mmask_i64gather_epi64(__m128i v1_old, __mmask8 mask, __m128i index, void const *addr, const int scale) |
|
_mm256_i64gather_epi64
__m256i _mm256_i64gather_epi64(long long const *m, __m256i i, const int s) |
|
_mm256_mask_i64gather_epi64
__m256i _mm256_mask_i64gather_epi64(__m256i a, long long const *m, __m256i i, __m256i mask, const int s) |
|
_mm256_mmask_i64gather_epi64
__m256i _mm256_mmask_i64gather_epi64(__m256i v1_old, __mmask8 mask, __m256i index, void const *addr, const int scale) |
|
_mm512_i64gather_epi64
__m512i _mm512_i64gather_epi64(__m512i index, void const *addr, const int scale) |
|
_mm512_mask_i64gather_epi64
__m512i _mm512_mask_i64gather_epi64(__m512i v1_old, __mmask8 mask, __m512i index, void const *addr, 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.
More AVX2 instructions
- VPBROADCASTB
- VPBROADCASTD
- VPBROADCASTQ
- VPBROADCASTW
- VPCMPEQB
- VPCMPEQD
- VPCMPEQQ
- VPCMPEQW
- VPCMPGTB
- VPCMPGTD
- VPCMPGTQ
- VPCMPGTW
- VPERM2I128
- VPERMD
- VPERMPD
- VPERMPS
- VPERMQ
- VPGATHERDD
- VPGATHERDQ
- VPGATHERQD
- VPHADDD
- VPHADDSW
- VPHADDW
- VPHSUBD
- VPHSUBSW
- VPHSUBW
- VPMADDUBSW
- VPMADDWD
- VPMASKMOVD
- VPMASKMOVQ
- VPMAXSB
- VPMAXSD
- VPMAXSW
- VPMAXUB
- VPMAXUD
- VPMAXUW
- VPMINSB
- VPMINSD
- VPMINSW
- VPMINUB
More AVX10.1 instructions
- VPERMPS
- VPERMQ
- VPERMT2B
- VPERMT2D
- VPERMT2PD
- VPERMT2PS
- VPERMT2Q
- VPERMT2W
- VPERMW
- VPEXPANDB
- VPEXPANDD
- VPEXPANDQ
- VPEXPANDW
- VPEXTRB
- VPEXTRD
- VPEXTRQ
- VPEXTRW
- VPGATHERDD
- VPGATHERDQ
- VPGATHERQD
- VPINSRB
- VPINSRD
- VPINSRQ
- VPINSRW
- VPLZCNTD
- VPLZCNTQ
- VPMADD52HUQ
- VPMADD52LUQ
- VPMADDUBSW
- VPMADDWD
- VPMAXSB
- VPMAXSD
- VPMAXSQ
- VPMAXSW
- VPMAXUB
- VPMAXUD
- VPMAXUQ
- VPMAXUW
- VPMINSB
- VPMINSD
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 64 and IA-32 Architectures Software Developer's Manual, Volume 2 (325383-093, September 2026): Volume 2C, page 5-555 (VPGATHERDQ/
VPGATHERQQ) ; Volume 2C, page 5-559 (VPGATHERQD/VPGATHERQQ) - Intel Advanced Vector Extensions 10.2 Architecture Specification, revision 7.0 (361050-007, April 2026)
- Intel 64 and IA-32 Architectures Optimization Reference Manual, Volume 1 (248966-051, October 2026)
- Software Optimization Guide for the AMD Zen5 Microarchitecture (58455, rev. 1.00, August 2024), Wayback Machine copy of AMD's ZIP
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.