Project

General

Profile

Statistics
| Revision:

root / lab4 / .minix-src / include / clang-3.6 / avx512vlintrin.h @ 13

History | View | Annotate | Download (3.57 KB)

1 13 up20180614
/*===---- avx512vlintrin.h - AVX512VL intrinsics ---------------------------===
2
 *
3
 * Permission is hereby granted, free of charge, to any person obtaining a copy
4
 * of this software and associated documentation files (the "Software"), to deal
5
 * in the Software without restriction, including without limitation the rights
6
 * to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
7
 * copies of the Software, and to permit persons to whom the Software is
8
 * furnished to do so, subject to the following conditions:
9
 *
10
 * The above copyright notice and this permission notice shall be included in
11
 * all copies or substantial portions of the Software.
12
 *
13
 * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
14
 * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
15
 * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
16
 * AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
17
 * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
18
 * OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
19
 * THE SOFTWARE.
20
 *
21
 *===-----------------------------------------------------------------------===
22
 */
23
24
#ifndef __IMMINTRIN_H
25
#error "Never use <avx512vlintrin.h> directly; include <immintrin.h> instead."
26
#endif
27
28
#ifndef __AVX512VLINTRIN_H
29
#define __AVX512VLINTRIN_H
30
31
/* Integer compare */
32
33
static __inline__ __mmask8 __attribute__((__always_inline__, __nodebug__))
34
_mm_cmpeq_epi32_mask(__m128i __a, __m128i __b) {
35
  return (__mmask8)__builtin_ia32_pcmpeqd128_mask((__v4si)__a, (__v4si)__b,
36
                                                  (__mmask8)-1);
37
}
38
39
static __inline__ __mmask8 __attribute__((__always_inline__, __nodebug__))
40
_mm_mask_cmpeq_epi32_mask(__mmask8 __u, __m128i __a, __m128i __b) {
41
  return (__mmask8)__builtin_ia32_pcmpeqd128_mask((__v4si)__a, (__v4si)__b,
42
                                                  __u);
43
}
44
45
46
static __inline__ __mmask8 __attribute__((__always_inline__, __nodebug__))
47
_mm256_cmpeq_epi32_mask(__m256i __a, __m256i __b) {
48
  return (__mmask8)__builtin_ia32_pcmpeqd256_mask((__v8si)__a, (__v8si)__b,
49
                                                  (__mmask8)-1);
50
}
51
52
static __inline__ __mmask8 __attribute__((__always_inline__, __nodebug__))
53
_mm256_mask_cmpeq_epi32_mask(__mmask8 __u, __m256i __a, __m256i __b) {
54
  return (__mmask8)__builtin_ia32_pcmpeqd256_mask((__v8si)__a, (__v8si)__b,
55
                                                  __u);
56
}
57
58
static __inline__ __mmask8 __attribute__((__always_inline__, __nodebug__))
59
_mm_cmpeq_epi64_mask(__m128i __a, __m128i __b) {
60
  return (__mmask8)__builtin_ia32_pcmpeqq128_mask((__v2di)__a, (__v2di)__b,
61
                                                  (__mmask8)-1);
62
}
63
64
static __inline__ __mmask8 __attribute__((__always_inline__, __nodebug__))
65
_mm_mask_cmpeq_epi64_mask(__mmask8 __u, __m128i __a, __m128i __b) {
66
  return (__mmask8)__builtin_ia32_pcmpeqq128_mask((__v2di)__a, (__v2di)__b,
67
                                                  __u);
68
}
69
70
71
static __inline__ __mmask8 __attribute__((__always_inline__, __nodebug__))
72
_mm256_cmpeq_epi64_mask(__m256i __a, __m256i __b) {
73
  return (__mmask8)__builtin_ia32_pcmpeqq256_mask((__v4di)__a, (__v4di)__b,
74
                                                  (__mmask8)-1);
75
}
76
77
static __inline__ __mmask8 __attribute__((__always_inline__, __nodebug__))
78
_mm256_mask_cmpeq_epi64_mask(__mmask8 __u, __m256i __a, __m256i __b) {
79
  return (__mmask8)__builtin_ia32_pcmpeqq256_mask((__v4di)__a, (__v4di)__b,
80
                                                  __u);
81
}
82
83
#endif /* __AVX512VLINTRIN_H */