1/*===------- avx512vpintersectintrin.h - VP2INTERSECT intrinsics ------------===
 2 *
 3 *
 4 * Permission is hereby granted, free of charge, to any person obtaining a copy
 5 * of this software and associated documentation files (the "Software"), to deal
 6 * in the Software without restriction, including without limitation the rights
 7 * to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
 8 * copies of the Software, and to permit persons to whom the Software is
 9 * furnished to do so, subject to the following conditions:
10 *
11 * The above copyright notice and this permission notice shall be included in
12 * all copies or substantial portions of the Software.
13 *
14 * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
15 * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
16 * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
17 * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
18 * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
19 * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
20 * THE SOFTWARE.
21 *
22 *===-----------------------------------------------------------------------===
23 */
24#ifndef __IMMINTRIN_H
25#error "Never use <avx512vp2intersect.h> directly; include <immintrin.h> instead."
26#endif
27
28#ifndef _AVX512VP2INTERSECT_H
29#define _AVX512VP2INTERSECT_H
30
31#define __DEFAULT_FN_ATTRS                                                     \
32  __attribute__((__always_inline__, __nodebug__,                               \
33                 __target__("avx512vp2intersect,evex512"),                     \
34                 __min_vector_width__(512)))
35
36/// Store, in an even/odd pair of mask registers, the indicators of the
37/// locations of value matches between dwords in operands __a and __b.
38///
39/// \headerfile <x86intrin.h>
40///
41/// This intrinsic corresponds to the <c> VP2INTERSECTD </c> instruction.
42///
43/// \param __a
44///    A 512-bit vector of [16 x i32].
45/// \param __b
46///    A 512-bit vector of [16 x i32]
47/// \param __m0
48///    A pointer point to 16-bit mask
49/// \param __m1
50///    A pointer point to 16-bit mask
51static __inline__ void __DEFAULT_FN_ATTRS
52_mm512_2intersect_epi32(__m512i __a, __m512i __b, __mmask16 *__m0, __mmask16 *__m1) {
53  __builtin_ia32_vp2intersect_d_512((__v16si)__a, (__v16si)__b, __m0, __m1);
54}
55
56/// Store, in an even/odd pair of mask registers, the indicators of the
57/// locations of value matches between quadwords in operands __a and __b.
58///
59/// \headerfile <x86intrin.h>
60///
61/// This intrinsic corresponds to the <c> VP2INTERSECTQ </c> instruction.
62///
63/// \param __a
64///    A 512-bit vector of [8 x i64].
65/// \param __b
66///    A 512-bit vector of [8 x i64]
67/// \param __m0
68///    A pointer point to 8-bit mask
69/// \param __m1
70///    A pointer point to 8-bit mask
71static __inline__ void __DEFAULT_FN_ATTRS
72_mm512_2intersect_epi64(__m512i __a, __m512i __b, __mmask8 *__m0, __mmask8 *__m1) {
73  __builtin_ia32_vp2intersect_q_512((__v8di)__a, (__v8di)__b, __m0, __m1);
74}
75
76#undef __DEFAULT_FN_ATTRS
77
78#endif