/src/zlib-ng/arch/x86/chunkset_avx2.c
Line | Count | Source |
1 | | /* chunkset_avx2.c -- AVX2 inline functions to copy small data chunks. |
2 | | * For conditions of distribution and use, see copyright notice in zlib.h |
3 | | */ |
4 | | |
5 | | #ifdef X86_AVX2 |
6 | | |
7 | | #include "zbuild.h" |
8 | | #include "zsanitizer.h" |
9 | | #include "zmemory.h" |
10 | | |
11 | | #include "arch/shared/chunk_256bit_perm_idx_lut.h" |
12 | | #include <immintrin.h> |
13 | | #include "x86_intrins.h" |
14 | | |
15 | | typedef __m256i chunk_t; |
16 | | typedef __m128i halfchunk_t; |
17 | | |
18 | | #define HAVE_CHUNKMEMSET_1 |
19 | | #define HAVE_CHUNKMEMSET_2 |
20 | | #define HAVE_CHUNKMEMSET_4 |
21 | | #define HAVE_CHUNKMEMSET_8 |
22 | | #define HAVE_CHUNKMEMSET_16 |
23 | | #define HAVE_CHUNK_MAG |
24 | | #define HAVE_HALF_CHUNK |
25 | | |
26 | 645k | static inline void chunkmemset_1(uint8_t *from, chunk_t *chunk) { |
27 | 645k | *chunk = _mm256_set1_epi8(*from); |
28 | 645k | } |
29 | | |
30 | 188k | static inline void chunkmemset_2(uint8_t *from, chunk_t *chunk) { |
31 | 188k | *chunk = _mm256_set1_epi16(zng_memread_2(from)); |
32 | 188k | } |
33 | | |
34 | 66.8k | static inline void chunkmemset_4(uint8_t *from, chunk_t *chunk) { |
35 | 66.8k | *chunk = _mm256_set1_epi32(zng_memread_4(from)); |
36 | 66.8k | } |
37 | | |
38 | 4.92k | static inline void chunkmemset_8(uint8_t *from, chunk_t *chunk) { |
39 | 4.92k | *chunk = _mm256_set1_epi64x(zng_memread_8(from)); |
40 | 4.92k | } |
41 | | |
42 | 1.70k | static inline void chunkmemset_16(uint8_t *from, chunk_t *chunk) { |
43 | | /* See explanation in chunkset_avx512.c */ |
44 | | #if defined(_MSC_VER) && _MSC_VER < 1920 |
45 | | halfchunk_t half = _mm_loadu_si128((__m128i*)from); |
46 | | *chunk = _mm256_inserti128_si256(_mm256_castsi128_si256(half), half, 1); |
47 | | #else |
48 | 1.70k | *chunk = _mm256_broadcastsi128_si256(_mm_loadu_si128((__m128i*)from)); |
49 | 1.70k | #endif |
50 | 1.70k | } |
51 | | |
52 | 23.6M | static inline void loadchunk(uint8_t const *s, chunk_t *chunk) { |
53 | 23.6M | *chunk = _mm256_loadu_si256((__m256i *)s); |
54 | 23.6M | } |
55 | | |
56 | 27.3M | static inline void storechunk(uint8_t *out, chunk_t *chunk) { |
57 | 27.3M | _mm256_storeu_si256((__m256i *)out, *chunk); |
58 | 27.3M | } |
59 | | |
60 | 286k | static inline chunk_t GET_CHUNK_MAG(uint8_t *buf, size_t *chunk_rem, size_t dist) { |
61 | 286k | lut_rem_pair lut_rem = perm_idx_lut[dist - 3]; |
62 | 286k | __m256i ret_vec; |
63 | | /* While technically we only need to read 4 or 8 bytes into this vector register for a lot of cases, GCC is |
64 | | * compiling this to a shared load for all branches, preferring the simpler code. Given that the buf value isn't in |
65 | | * GPRs to begin with the 256 bit load is _probably_ just as inexpensive */ |
66 | 286k | *chunk_rem = lut_rem.remval; |
67 | | |
68 | | /* See note in chunkset_ssse3.c for why this is ok */ |
69 | 286k | __msan_unpoison(buf + dist, 32 - dist); |
70 | | |
71 | 286k | if (dist < 16) { |
72 | | /* This simpler case still requires us to shuffle in 128 bit lanes, so we must apply a static offset after |
73 | | * broadcasting the first vector register to both halves. This is _marginally_ faster than doing two separate |
74 | | * shuffles and combining the halves later */ |
75 | 229k | __m256i perm_vec = _mm256_load_si256((__m256i*)(permute_table+lut_rem.idx)); |
76 | 229k | __m128i ret_vec0 = _mm_loadu_si128((__m128i*)buf); |
77 | 229k | ret_vec = _mm256_inserti128_si256(_mm256_castsi128_si256(ret_vec0), ret_vec0, 1); |
78 | 229k | ret_vec = _mm256_shuffle_epi8(ret_vec, perm_vec); |
79 | 229k | } else { |
80 | 56.6k | __m128i ret_vec0 = _mm_loadu_si128((__m128i*)buf); |
81 | 56.6k | __m128i ret_vec1 = _mm_loadu_si128((__m128i*)(buf + 16)); |
82 | | /* Take advantage of the fact that only the latter half of the 256 bit vector will actually differ */ |
83 | 56.6k | __m128i perm_vec1 = _mm_load_si128((__m128i*)(permute_table + lut_rem.idx)); |
84 | 56.6k | __m128i xlane_permutes = _mm_cmpgt_epi8(_mm_set1_epi8(16), perm_vec1); |
85 | 56.6k | __m128i xlane_res = _mm_shuffle_epi8(ret_vec0, perm_vec1); |
86 | | /* Since we can't wrap twice, we can simply keep the later half exactly how it is instead of having to _also_ |
87 | | * shuffle those values */ |
88 | 56.6k | __m128i latter_half = _mm_blendv_epi8(ret_vec1, xlane_res, xlane_permutes); |
89 | 56.6k | ret_vec = _mm256_inserti128_si256(_mm256_castsi128_si256(ret_vec0), latter_half, 1); |
90 | 56.6k | } |
91 | | |
92 | 286k | return ret_vec; |
93 | 286k | } |
94 | | |
95 | 0 | static inline void loadhalfchunk(uint8_t const *s, halfchunk_t *chunk) { |
96 | 0 | *chunk = _mm_loadu_si128((__m128i *)s); |
97 | 0 | } |
98 | | |
99 | 947 | static inline void storehalfchunk(uint8_t *out, halfchunk_t *chunk) { |
100 | 947 | _mm_storeu_si128((__m128i *)out, *chunk); |
101 | 947 | } |
102 | | |
103 | 70.0k | static inline chunk_t halfchunk2whole(halfchunk_t *chunk) { |
104 | | /* We zero extend mostly to appease some memory sanitizers. These bytes are ultimately |
105 | | * unlikely to be actually written or read from */ |
106 | 70.0k | return _mm256_zextsi128_si256(*chunk); |
107 | 70.0k | } |
108 | | |
109 | 70.0k | static inline halfchunk_t GET_HALFCHUNK_MAG(uint8_t *buf, size_t *chunk_rem, size_t dist) { |
110 | 70.0k | lut_rem_pair lut_rem = perm_idx_lut[dist - 3]; |
111 | 70.0k | __m128i perm_vec, ret_vec; |
112 | 70.0k | __msan_unpoison(buf + dist, 16 - dist); |
113 | 70.0k | ret_vec = _mm_loadu_si128((__m128i*)buf); |
114 | 70.0k | *chunk_rem = half_rem_vals[dist - 3]; |
115 | | |
116 | 70.0k | perm_vec = _mm_load_si128((__m128i*)(permute_table + lut_rem.idx)); |
117 | 70.0k | ret_vec = _mm_shuffle_epi8(ret_vec, perm_vec); |
118 | | |
119 | 70.0k | return ret_vec; |
120 | 70.0k | } |
121 | | |
122 | | #define CHUNKSIZE chunksize_avx2 |
123 | 16.2M | #define CHUNKCOPY chunkcopy_avx2 |
124 | 0 | #define CHUNKUNROLL chunkunroll_avx2 |
125 | 1.26M | #define CHUNKMEMSET chunkmemset_avx2 |
126 | | #define CHUNKMEMSET_SAFE chunkmemset_safe_avx2 |
127 | | |
128 | | #include "chunkset_tpl.h" |
129 | | |
130 | | #define INFLATE_FAST inflate_fast_avx2 |
131 | | |
132 | | #include "inffast_tpl.h" |
133 | | |
134 | | #endif |