133 lines
6.3 KiB
HTML
133 lines
6.3 KiB
HTML
|
<!DOCTYPE html>
|
|||
|
|
<html xmlns="http://www.w3.org/1999/xhtml" xmlns:svg="http://www.w3.org/2000/svg" xmlns:x86="http://www.felixcloutier.com/x86"><head><meta http-equiv="Content-Type" content="text/html; charset=UTF-8"><link rel="stylesheet" type="text/css" href="style.css"></link><title>VP2INTERSECTD/VP2INTERSECTQ
|
|||
|
|
— Compute Intersection Between DWORDS/QUADWORDS to aPair of Mask Registers</title></head><body><header><nav><ul><li><a href='index.html'>Index</a></li><li>December 2023</li></ul></nav></header><h1>VP2INTERSECTD/VP2INTERSECTQ
|
|||
|
|
— Compute Intersection Between DWORDS/QUADWORDS to aPair of Mask Registers</h1>
|
|||
|
|
|
|||
|
|
|
|||
|
|
<table>
|
|||
|
|
<tr>
|
|||
|
|
<th>Opcode/Instruction</th>
|
|||
|
|
<th>Op/En</th>
|
|||
|
|
<th>64/32 bit Mode Support</th>
|
|||
|
|
<th>CPUID Feature Flag</th>
|
|||
|
|
<th>Description</th></tr>
|
|||
|
|
<tr>
|
|||
|
|
<td>EVEX.NDS.128.F2.0F38.W0 68 /r VP2INTERSECTD k1+1, xmm2, xmm3/m128/m32bcst</td>
|
|||
|
|
<td>A</td>
|
|||
|
|
<td>V/V</td>
|
|||
|
|
<td>AVX512VL AVX512_VP2INTERSECT</td>
|
|||
|
|
<td>Store, in an even/odd pair of mask registers, the indicators of the locations of value matches between dwords in xmm3/m128/m32bcst and xmm2.</td></tr>
|
|||
|
|
<tr>
|
|||
|
|
<td>EVEX.NDS.256.F2.0F38.W0 68 /r VP2INTERSECTD k1+1, ymm2, ymm3/m256/m32bcst</td>
|
|||
|
|
<td>A</td>
|
|||
|
|
<td>V/V</td>
|
|||
|
|
<td>AVX512VL AVX512_VP2INTERSECT</td>
|
|||
|
|
<td>Store, in an even/odd pair of mask registers, the indicators of the locations of value matches between dwords in ymm3/m256/m32bcst and ymm2.</td></tr>
|
|||
|
|
<tr>
|
|||
|
|
<td>EVEX.NDS.512.F2.0F38.W0 68 /r VP2INTERSECTD k1+1, zmm2, zmm3/m512/m32bcst</td>
|
|||
|
|
<td>A</td>
|
|||
|
|
<td>V/V</td>
|
|||
|
|
<td>AVX512F AVX512_VP2INTERSECT</td>
|
|||
|
|
<td>Store, in an even/odd pair of mask registers, the indicators of the locations of value matches between dwords in zmm3/m512/m32bcst and zmm2.</td></tr>
|
|||
|
|
<tr>
|
|||
|
|
<td>EVEX.NDS.128.F2.0F38.W1 68 /r VP2INTERSECTQ k1+1, xmm2, xmm3/m128/m64bcst</td>
|
|||
|
|
<td>A</td>
|
|||
|
|
<td>V/V</td>
|
|||
|
|
<td>AVX512VL AVX512_VP2INTERSECT</td>
|
|||
|
|
<td>Store, in an even/odd pair of mask registers, the indicators of the locations of value matches between quadwords in xmm3/m128/m64bcst and xmm2.</td></tr>
|
|||
|
|
<tr>
|
|||
|
|
<td>EVEX.NDS.256.F2.0F38.W1 68 /r VP2INTERSECTQ k1+1, ymm2, ymm3/m256/m64bcst</td>
|
|||
|
|
<td>A</td>
|
|||
|
|
<td>V/V</td>
|
|||
|
|
<td>AVX512VL AVX512_VP2INTERSECT</td>
|
|||
|
|
<td>Store, in an even/odd pair of mask registers, the indicators of the locations of value matches between quadwords in ymm3/m256/m64bcst and ymm2.</td></tr>
|
|||
|
|
<tr>
|
|||
|
|
<td>EVEX.NDS.512.F2.0F38.W1 68 /r VP2INTERSECTQ k1+1, zmm2, zmm3/m512/m64bcst</td>
|
|||
|
|
<td>A</td>
|
|||
|
|
<td>V/V</td>
|
|||
|
|
<td>AVX512F AVX512_VP2INTERSECT</td>
|
|||
|
|
<td>Store, in an even/odd pair of mask registers, the indicators of the locations of value matches between quadwords in zmm3/m512/m64bcst and zmm2.</td></tr></table>
|
|||
|
|
<h2 id="instruction-operand-encoding">Instruction Operand Encoding<a class="anchor" href="#instruction-operand-encoding">
|
|||
|
|
¶
|
|||
|
|
</a></h2>
|
|||
|
|
<table>
|
|||
|
|
<tr>
|
|||
|
|
<th>Op/En</th>
|
|||
|
|
<th>Tuple</th>
|
|||
|
|
<th>Operand 1</th>
|
|||
|
|
<th>Operand 2</th>
|
|||
|
|
<th>Operand 3</th>
|
|||
|
|
<th>Operand 4</th></tr>
|
|||
|
|
<tr>
|
|||
|
|
<td>A</td>
|
|||
|
|
<td>Full</td>
|
|||
|
|
<td>ModRM:reg (w)</td>
|
|||
|
|
<td>EVEX.vvvv (r)</td>
|
|||
|
|
<td>ModRM:r/m (r)</td>
|
|||
|
|
<td>N/A</td></tr></table>
|
|||
|
|
<h3 id="description">Description<a class="anchor" href="#description">
|
|||
|
|
¶
|
|||
|
|
</a></h3>
|
|||
|
|
<p>This instruction writes an even/odd pair of mask registers. The mask register destination indicated in the MODRM.REG field is used to form the basis of the register pair. The low bit of that field is masked off (set to zero) to create the first register of the pair.</p>
|
|||
|
|
<p>EVEX.aaa and EVEX.z must be zero.</p>
|
|||
|
|
<h3 id="operation">Operation<a class="anchor" href="#operation">
|
|||
|
|
¶
|
|||
|
|
</a></h3>
|
|||
|
|
<h4 id="vp2intersectd-destmask--src1--src2">VP2INTERSECTD destmask, src1, src2<a class="anchor" href="#vp2intersectd-destmask--src1--src2">
|
|||
|
|
¶
|
|||
|
|
</a></h4>
|
|||
|
|
<pre>(KL, VL) = (4, 128), (8, 256), (16, 512)
|
|||
|
|
// dest_mask_reg_id is the register id specified in the instruction for destmask
|
|||
|
|
dest_base := dest_mask_reg_id & ~1
|
|||
|
|
// maskregs[ ] is an array representing the mask registers
|
|||
|
|
maskregs[dest_base+0][MAX_KL-1:0] := 0
|
|||
|
|
maskregs[dest_base+1][MAX_KL-1:0] := 0
|
|||
|
|
FOR i := 0 to KL-1:
|
|||
|
|
FOR j := 0 to KL-1:
|
|||
|
|
match := (src1.dword[i] == src2.dword[j])
|
|||
|
|
maskregs[dest_base+0].bit[i] |= match
|
|||
|
|
maskregs[dest_base+1].bit[j] |= match
|
|||
|
|
</pre>
|
|||
|
|
<h4 id="vp2intersectq-destmask--src1--src2">VP2INTERSECTQ destmask, src1, src2<a class="anchor" href="#vp2intersectq-destmask--src1--src2">
|
|||
|
|
¶
|
|||
|
|
</a></h4>
|
|||
|
|
<pre>(KL, VL) = (2, 128), (4, 256), (8, 512)
|
|||
|
|
// dest_mask_reg_id is the register id specified in the instruction for destmask
|
|||
|
|
dest_base := dest_mask_reg_id & ~1
|
|||
|
|
// maskregs[ ] is an array representing the mask registers
|
|||
|
|
maskregs[dest_base+0][MAX_KL-1:0] := 0
|
|||
|
|
maskregs[dest_base+1][MAX_KL-1:0] := 0
|
|||
|
|
FOR i = 0 to KL-1:
|
|||
|
|
FOR j = 0 to KL-1:
|
|||
|
|
match := (src1.qword[i] == src2.qword[j])
|
|||
|
|
maskregs[dest_base+0].bit[i] |= match
|
|||
|
|
maskregs[dest_base+1].bit[j] |= match
|
|||
|
|
</pre>
|
|||
|
|
<h3 id="intel-c-c++-compiler-intrinsic-equivalent">Intel C/C++ Compiler Intrinsic Equivalent<a class="anchor" href="#intel-c-c++-compiler-intrinsic-equivalent">
|
|||
|
|
¶
|
|||
|
|
</a></h3>
|
|||
|
|
<pre>VP2INTERSECTD void _mm_2intersect_epi32(__m128i, __m128i, __mmask8 *, __mmask8 *);
|
|||
|
|
</pre>
|
|||
|
|
<pre>VP2INTERSECTD void _mm256_2intersect_epi32(__m256i, __m256i, __mmask8 *, __mmask8 *);
|
|||
|
|
</pre>
|
|||
|
|
<pre>VP2INTERSECTD void _mm512_2intersect_epi32(__m512i, __m512i, __mmask16 *, __mmask16 *);
|
|||
|
|
</pre>
|
|||
|
|
<pre>VP2INTERSECTQ void _mm_2intersect_epi64(__m128i, __m128i, __mmask8 *, __mmask8 *);
|
|||
|
|
</pre>
|
|||
|
|
<pre>VP2INTERSECTQ void _mm256_2intersect_epi64(__m256i, __m256i, __mmask8 *, __mmask8 *);
|
|||
|
|
</pre>
|
|||
|
|
<pre>VP2INTERSECTQ void _mm512_2intersect_epi64(__m512i, __m512i, __mmask8 *, __mmask8 *);
|
|||
|
|
</pre>
|
|||
|
|
<h3 class="exceptions" id="simd-floating-point-exceptions">SIMD Floating-Point Exceptions<a class="anchor" href="#simd-floating-point-exceptions">
|
|||
|
|
¶
|
|||
|
|
</a></h3>
|
|||
|
|
<p>None.</p>
|
|||
|
|
<h3 class="exceptions" id="other-exceptions">Other Exceptions<a class="anchor" href="#other-exceptions">
|
|||
|
|
¶
|
|||
|
|
</a></h3>
|
|||
|
|
<p>See <span class="not-imported">Table 2-50</span>, “Type E4NF Class Exception Conditions.”</p><footer><p>
|
|||
|
|
This UNOFFICIAL, mechanically-separated, non-verified reference is provided for convenience, but it may be
|
|||
|
|
inc<span style="opacity: 0.2">omp</span>lete or b<sub>r</sub>oke<sub>n</sub> in various obvious or non-obvious
|
|||
|
|
ways. Refer to <a href="https://software.intel.com/en-us/download/intel-64-and-ia-32-architectures-sdm-combined-volumes-1-2a-2b-2c-2d-3a-3b-3c-3d-and-4">Intel® 64 and IA-32 Architectures Software Developer’s Manual</a> for anything serious.
|
|||
|
|
</p></footer></body></html>
|