LMMS
Loading...
Searching...
No Matches
juce_avx_SIMDNativeOps.h
Go to the documentation of this file.
1/*
2 ==============================================================================
3
4 This file is part of the JUCE library.
5 Copyright (c) 2022 - Raw Material Software Limited
6
7 JUCE is an open source library subject to commercial or open-source
8 licensing.
9
10 By using JUCE, you agree to the terms of both the JUCE 7 End-User License
11 Agreement and JUCE Privacy Policy.
12
13 End User License Agreement: www.juce.com/juce-7-licence
14 Privacy Policy: www.juce.com/juce-privacy-policy
15
16 Or: You may also use this code under the terms of the GPL v3 (see
17 www.gnu.org/licenses).
18
19 JUCE IS PROVIDED "AS IS" WITHOUT ANY WARRANTY, AND ALL WARRANTIES, WHETHER
20 EXPRESSED OR IMPLIED, INCLUDING MERCHANTABILITY AND FITNESS FOR PURPOSE, ARE
21 DISCLAIMED.
22
23 ==============================================================================
24*/
25
26namespace juce
27{
28namespace dsp
29{
30
31#ifndef DOXYGEN
32
33JUCE_BEGIN_IGNORE_WARNINGS_GCC_LIKE ("-Wignored-attributes")
34
35#ifdef _MSC_VER
36 #define DECLARE_AVX_SIMD_CONST(type, name) \
37 static __declspec(align(32)) const type name[32 / sizeof (type)]
38
39 #define DEFINE_AVX_SIMD_CONST(type, class_type, name) \
40 __declspec(align(32)) const type SIMDNativeOps<class_type>:: name[32 / sizeof (type)]
41
42#else
43 #define DECLARE_AVX_SIMD_CONST(type, name) \
44 static const type name[32 / sizeof (type)] __attribute__((aligned(32)))
45
46 #define DEFINE_AVX_SIMD_CONST(type, class_type, name) \
47 const type SIMDNativeOps<class_type>:: name[32 / sizeof (type)] __attribute__((aligned(32)))
48
49#endif
50
51template <typename type>
52struct SIMDNativeOps;
53
54//==============================================================================
59template <>
60struct SIMDNativeOps<float>
61{
62 using vSIMDType = __m256;
63
64 //==============================================================================
65 DECLARE_AVX_SIMD_CONST (int32_t, kAllBitsSet);
66 DECLARE_AVX_SIMD_CONST (int32_t, kEvenHighBit);
67 DECLARE_AVX_SIMD_CONST (float, kOne);
68
69 //==============================================================================
70 static forcedinline __m256 JUCE_VECTOR_CALLTYPE vconst (const float* a) noexcept { return load (a); }
71 static forcedinline __m256 JUCE_VECTOR_CALLTYPE vconst (const int32_t* a) noexcept { return _mm256_castsi256_ps (_mm256_load_si256 (reinterpret_cast <const __m256i*> (a))); }
72 static forcedinline __m256 JUCE_VECTOR_CALLTYPE expand (float s) noexcept { return _mm256_broadcast_ss (&s); }
73 static forcedinline __m256 JUCE_VECTOR_CALLTYPE load (const float* a) noexcept { return _mm256_load_ps (a); }
74 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256 value, float* dest) noexcept { _mm256_store_ps (dest, value); }
75 static forcedinline __m256 JUCE_VECTOR_CALLTYPE add (__m256 a, __m256 b) noexcept { return _mm256_add_ps (a, b); }
76 static forcedinline __m256 JUCE_VECTOR_CALLTYPE sub (__m256 a, __m256 b) noexcept { return _mm256_sub_ps (a, b); }
77 static forcedinline __m256 JUCE_VECTOR_CALLTYPE mul (__m256 a, __m256 b) noexcept { return _mm256_mul_ps (a, b); }
78 static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_and (__m256 a, __m256 b) noexcept { return _mm256_and_ps (a, b); }
79 static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_or (__m256 a, __m256 b) noexcept { return _mm256_or_ps (a, b); }
80 static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_xor (__m256 a, __m256 b) noexcept { return _mm256_xor_ps (a, b); }
81 static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_notand (__m256 a, __m256 b) noexcept { return _mm256_andnot_ps (a, b); }
82 static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_not (__m256 a) noexcept { return bit_notand (a, vconst (kAllBitsSet)); }
83 static forcedinline __m256 JUCE_VECTOR_CALLTYPE min (__m256 a, __m256 b) noexcept { return _mm256_min_ps (a, b); }
84 static forcedinline __m256 JUCE_VECTOR_CALLTYPE max (__m256 a, __m256 b) noexcept { return _mm256_max_ps (a, b); }
85 static forcedinline __m256 JUCE_VECTOR_CALLTYPE equal (__m256 a, __m256 b) noexcept { return _mm256_cmp_ps (a, b, _CMP_EQ_OQ); }
86 static forcedinline __m256 JUCE_VECTOR_CALLTYPE notEqual (__m256 a, __m256 b) noexcept { return _mm256_cmp_ps (a, b, _CMP_NEQ_OQ); }
87 static forcedinline __m256 JUCE_VECTOR_CALLTYPE greaterThan (__m256 a, __m256 b) noexcept { return _mm256_cmp_ps (a, b, _CMP_GT_OQ); }
88 static forcedinline __m256 JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256 a, __m256 b) noexcept { return _mm256_cmp_ps (a, b, _CMP_GE_OQ); }
89 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256 a, __m256 b) noexcept { return (_mm256_movemask_ps (equal (a, b)) == 0xff); }
90 static forcedinline __m256 JUCE_VECTOR_CALLTYPE dupeven (__m256 a) noexcept { return _mm256_shuffle_ps (a, a, _MM_SHUFFLE (2, 2, 0, 0)); }
91 static forcedinline __m256 JUCE_VECTOR_CALLTYPE dupodd (__m256 a) noexcept { return _mm256_shuffle_ps (a, a, _MM_SHUFFLE (3, 3, 1, 1)); }
92 static forcedinline __m256 JUCE_VECTOR_CALLTYPE swapevenodd (__m256 a) noexcept { return _mm256_shuffle_ps (a, a, _MM_SHUFFLE (2, 3, 0, 1)); }
93 static forcedinline float JUCE_VECTOR_CALLTYPE get (__m256 v, size_t i) noexcept { return SIMDFallbackOps<float, __m256>::get (v, i); }
94 static forcedinline __m256 JUCE_VECTOR_CALLTYPE set (__m256 v, size_t i, float s) noexcept { return SIMDFallbackOps<float, __m256>::set (v, i, s); }
95 static forcedinline __m256 JUCE_VECTOR_CALLTYPE truncate (__m256 a) noexcept { return _mm256_cvtepi32_ps (_mm256_cvttps_epi32 (a)); }
96
97 static forcedinline __m256 JUCE_VECTOR_CALLTYPE multiplyAdd (__m256 a, __m256 b, __m256 c) noexcept
98 {
99 #if __FMA__
100 return _mm256_fmadd_ps (b, c, a);
101 #else
102 return add (a, mul (b, c));
103 #endif
104 }
105
106 static forcedinline __m256 JUCE_VECTOR_CALLTYPE oddevensum (__m256 a) noexcept
107 {
108 a = _mm256_add_ps (_mm256_shuffle_ps (a, a, _MM_SHUFFLE (1, 0, 3, 2)), a);
109 return add (_mm256_permute2f128_ps (a, a, 1), a);
110 }
111
112 //==============================================================================
113 static forcedinline __m256 JUCE_VECTOR_CALLTYPE cmplxmul (__m256 a, __m256 b) noexcept
114 {
115 __m256 rr_ir = mul (a, dupeven (b));
116 __m256 ii_ri = mul (swapevenodd (a), dupodd (b));
117 return add (rr_ir, bit_xor (ii_ri, vconst (kEvenHighBit)));
118 }
119
120 static forcedinline float JUCE_VECTOR_CALLTYPE sum (__m256 a) noexcept
121 {
122 __m256 retval = _mm256_dp_ps (a, vconst (kOne), 0xff);
123 __m256 tmp = _mm256_permute2f128_ps (retval, retval, 1);
124 retval = _mm256_add_ps (retval, tmp);
125
126 #if JUCE_GCC
127 return retval[0];
128 #else
129 return _mm256_cvtss_f32 (retval);
130 #endif
131 }
132};
133
134//==============================================================================
139template <>
140struct SIMDNativeOps<double>
141{
142 using vSIMDType = __m256d;
143
144 //==============================================================================
145 DECLARE_AVX_SIMD_CONST (int64_t, kAllBitsSet);
146 DECLARE_AVX_SIMD_CONST (int64_t, kEvenHighBit);
147 DECLARE_AVX_SIMD_CONST (double, kOne);
148
149 //==============================================================================
150 static forcedinline __m256d JUCE_VECTOR_CALLTYPE vconst (const double* a) noexcept { return load (a); }
151 static forcedinline __m256d JUCE_VECTOR_CALLTYPE vconst (const int64_t* a) noexcept { return _mm256_castsi256_pd (_mm256_load_si256 (reinterpret_cast <const __m256i*> (a))); }
152 static forcedinline __m256d JUCE_VECTOR_CALLTYPE expand (double s) noexcept { return _mm256_broadcast_sd (&s); }
153 static forcedinline __m256d JUCE_VECTOR_CALLTYPE load (const double* a) noexcept { return _mm256_load_pd (a); }
154 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256d value, double* dest) noexcept { _mm256_store_pd (dest, value); }
155 static forcedinline __m256d JUCE_VECTOR_CALLTYPE add (__m256d a, __m256d b) noexcept { return _mm256_add_pd (a, b); }
156 static forcedinline __m256d JUCE_VECTOR_CALLTYPE sub (__m256d a, __m256d b) noexcept { return _mm256_sub_pd (a, b); }
157 static forcedinline __m256d JUCE_VECTOR_CALLTYPE mul (__m256d a, __m256d b) noexcept { return _mm256_mul_pd (a, b); }
158 static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_and (__m256d a, __m256d b) noexcept { return _mm256_and_pd (a, b); }
159 static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_or (__m256d a, __m256d b) noexcept { return _mm256_or_pd (a, b); }
160 static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_xor (__m256d a, __m256d b) noexcept { return _mm256_xor_pd (a, b); }
161 static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_notand (__m256d a, __m256d b) noexcept { return _mm256_andnot_pd (a, b); }
162 static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_not (__m256d a) noexcept { return bit_notand (a, vconst (kAllBitsSet)); }
163 static forcedinline __m256d JUCE_VECTOR_CALLTYPE min (__m256d a, __m256d b) noexcept { return _mm256_min_pd (a, b); }
164 static forcedinline __m256d JUCE_VECTOR_CALLTYPE max (__m256d a, __m256d b) noexcept { return _mm256_max_pd (a, b); }
165 static forcedinline __m256d JUCE_VECTOR_CALLTYPE equal (__m256d a, __m256d b) noexcept { return _mm256_cmp_pd (a, b, _CMP_EQ_OQ); }
166 static forcedinline __m256d JUCE_VECTOR_CALLTYPE notEqual (__m256d a, __m256d b) noexcept { return _mm256_cmp_pd (a, b, _CMP_NEQ_OQ); }
167 static forcedinline __m256d JUCE_VECTOR_CALLTYPE greaterThan (__m256d a, __m256d b) noexcept { return _mm256_cmp_pd (a, b, _CMP_GT_OQ); }
168 static forcedinline __m256d JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256d a, __m256d b) noexcept { return _mm256_cmp_pd (a, b, _CMP_GE_OQ); }
169 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256d a, __m256d b) noexcept { return (_mm256_movemask_pd (equal (a, b)) == 0xf); }
170 static forcedinline __m256d JUCE_VECTOR_CALLTYPE multiplyAdd (__m256d a, __m256d b, __m256d c) noexcept { return _mm256_add_pd (a, _mm256_mul_pd (b, c)); }
171 static forcedinline __m256d JUCE_VECTOR_CALLTYPE dupeven (__m256d a) noexcept { return _mm256_shuffle_pd (a, a, 0); }
172 static forcedinline __m256d JUCE_VECTOR_CALLTYPE dupodd (__m256d a) noexcept { return _mm256_shuffle_pd (a, a, (1 << 0) | (1 << 1) | (1 << 2) | (1 << 3)); }
173 static forcedinline __m256d JUCE_VECTOR_CALLTYPE swapevenodd (__m256d a) noexcept { return _mm256_shuffle_pd (a, a, (1 << 0) | (0 << 1) | (1 << 2) | (0 << 3)); }
174 static forcedinline __m256d JUCE_VECTOR_CALLTYPE oddevensum (__m256d a) noexcept { return _mm256_add_pd (_mm256_permute2f128_pd (a, a, 1), a); }
175 static forcedinline double JUCE_VECTOR_CALLTYPE get (__m256d v, size_t i) noexcept { return SIMDFallbackOps<double, __m256d>::get (v, i); }
176 static forcedinline __m256d JUCE_VECTOR_CALLTYPE set (__m256d v, size_t i, double s) noexcept { return SIMDFallbackOps<double, __m256d>::set (v, i, s); }
177 static forcedinline __m256d JUCE_VECTOR_CALLTYPE truncate (__m256d a) noexcept { return _mm256_cvtepi32_pd (_mm256_cvttpd_epi32 (a)); }
178
179 //==============================================================================
180 static forcedinline __m256d JUCE_VECTOR_CALLTYPE cmplxmul (__m256d a, __m256d b) noexcept
181 {
182 __m256d rr_ir = mul (a, dupeven (b));
183 __m256d ii_ri = mul (swapevenodd (a), dupodd (b));
184 return add (rr_ir, bit_xor (ii_ri, vconst (kEvenHighBit)));
185 }
186
187 static forcedinline double JUCE_VECTOR_CALLTYPE sum (__m256d a) noexcept
188 {
189 __m256d retval = _mm256_hadd_pd (a, a);
190 __m256d tmp = _mm256_permute2f128_pd (retval, retval, 1);
191 retval = _mm256_add_pd (retval, tmp);
192
193 #if JUCE_GCC
194 return retval[0];
195 #else
196 return _mm256_cvtsd_f64 (retval);
197 #endif
198 }
199};
200
201//==============================================================================
206template <>
207struct SIMDNativeOps<int8_t>
208{
209 using vSIMDType = __m256i;
210
211 //==============================================================================
212 DECLARE_AVX_SIMD_CONST (int8_t, kAllBitsSet);
213
214 static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand (int8_t s) noexcept { return _mm256_set1_epi8 (s); }
215 static forcedinline __m256i JUCE_VECTOR_CALLTYPE load (const int8_t* p) noexcept { return _mm256_load_si256 (reinterpret_cast<const __m256i*> (p)); }
216 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256i value, int8_t* dest) noexcept { _mm256_store_si256 (reinterpret_cast<__m256i*> (dest), value); }
217 static forcedinline __m256i JUCE_VECTOR_CALLTYPE add (__m256i a, __m256i b) noexcept { return _mm256_add_epi8 (a, b); }
218 static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub (__m256i a, __m256i b) noexcept { return _mm256_sub_epi8 (a, b); }
219 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and (__m256i a, __m256i b) noexcept { return _mm256_and_si256 (a, b); }
220 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or (__m256i a, __m256i b) noexcept { return _mm256_or_si256 (a, b); }
221 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor (__m256i a, __m256i b) noexcept { return _mm256_xor_si256 (a, b); }
222 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot (__m256i a, __m256i b) noexcept { return _mm256_andnot_si256 (a, b); }
223 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not (__m256i a) noexcept { return _mm256_andnot_si256 (a, load (kAllBitsSet)); }
224 static forcedinline __m256i JUCE_VECTOR_CALLTYPE min (__m256i a, __m256i b) noexcept { return _mm256_min_epi8 (a, b); }
225 static forcedinline __m256i JUCE_VECTOR_CALLTYPE max (__m256i a, __m256i b) noexcept { return _mm256_max_epi8 (a, b); }
226 static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal (__m256i a, __m256i b) noexcept { return _mm256_cmpeq_epi8 (a, b); }
227 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan (__m256i a, __m256i b) noexcept { return _mm256_cmpgt_epi8 (a, b); }
228 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256i a, __m256i b) noexcept { return bit_or (greaterThan (a, b), equal (a,b)); }
229 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256i a, __m256i b) noexcept { return _mm256_movemask_epi8 (equal (a, b)) == -1; }
230 static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd (__m256i a, __m256i b, __m256i c) noexcept { return add (a, mul (b, c)); }
231 static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual (__m256i a, __m256i b) noexcept { return bit_not (equal (a, b)); }
232 static forcedinline int8_t JUCE_VECTOR_CALLTYPE get (__m256i v, size_t i) noexcept { return SIMDFallbackOps<int8_t, __m256i>::get (v, i); }
233 static forcedinline __m256i JUCE_VECTOR_CALLTYPE set (__m256i v, size_t i, int8_t s) noexcept { return SIMDFallbackOps<int8_t, __m256i>::set (v, i, s); }
234 static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate (__m256i a) noexcept { return a; }
235
236 //==============================================================================
237 static forcedinline int8_t JUCE_VECTOR_CALLTYPE sum (__m256i a) noexcept
238 {
239 __m256i lo = _mm256_unpacklo_epi8 (a, _mm256_setzero_si256());
240 __m256i hi = _mm256_unpackhi_epi8 (a, _mm256_setzero_si256());
241
242 for (int i = 0; i < 3; ++i)
243 {
244 lo = _mm256_hadd_epi16 (lo, lo);
245 hi = _mm256_hadd_epi16 (hi, hi);
246 }
247
248 #if JUCE_GCC
249 return (int8_t) ((lo[0] & 0xff) +
250 (hi[0] & 0xff) +
251 (lo[2] & 0xff) +
252 (hi[2] & 0xff));
253 #else
254 constexpr int mask = (2 << 0) | (3 << 2) | (0 << 4) | (1 << 6);
255
256 return (int8_t) ((_mm256_cvtsi256_si32 (lo) & 0xff) +
257 (_mm256_cvtsi256_si32 (hi) & 0xff) +
258 (_mm256_cvtsi256_si32 (_mm256_permute4x64_epi64 (lo, mask)) & 0xff) +
259 (_mm256_cvtsi256_si32 (_mm256_permute4x64_epi64 (hi, mask)) & 0xff));
260 #endif
261 }
262
263 static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul (__m256i a, __m256i b)
264 {
265 // unpack and multiply
266 __m256i even = _mm256_mullo_epi16 (a, b);
267 __m256i odd = _mm256_mullo_epi16 (_mm256_srli_epi16 (a, 8), _mm256_srli_epi16 (b, 8));
268
269 return _mm256_or_si256 (_mm256_slli_epi16 (odd, 8),
270 _mm256_srli_epi16 (_mm256_slli_epi16 (even, 8), 8));
271 }
272};
273
274//==============================================================================
279template <>
280struct SIMDNativeOps<uint8_t>
281{
282 //==============================================================================
283 using vSIMDType = __m256i;
284
285 //==============================================================================
286 DECLARE_AVX_SIMD_CONST (uint8_t, kHighBit);
287 DECLARE_AVX_SIMD_CONST (uint8_t, kAllBitsSet);
288
289 static forcedinline __m256i JUCE_VECTOR_CALLTYPE ssign (__m256i a) noexcept { return _mm256_xor_si256 (a, load (kHighBit)); }
290 static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand (uint8_t s) noexcept { return _mm256_set1_epi8 ((int8_t) s); }
291 static forcedinline __m256i JUCE_VECTOR_CALLTYPE load (const uint8_t* p) noexcept { return _mm256_load_si256 (reinterpret_cast<const __m256i*> (p)); }
292 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256i value, uint8_t* dest) noexcept { _mm256_store_si256 (reinterpret_cast<__m256i*> (dest), value); }
293 static forcedinline __m256i JUCE_VECTOR_CALLTYPE add (__m256i a, __m256i b) noexcept { return _mm256_add_epi8 (a, b); }
294 static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub (__m256i a, __m256i b) noexcept { return _mm256_sub_epi8 (a, b); }
295 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and (__m256i a, __m256i b) noexcept { return _mm256_and_si256 (a, b); }
296 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or (__m256i a, __m256i b) noexcept { return _mm256_or_si256 (a, b); }
297 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor (__m256i a, __m256i b) noexcept { return _mm256_xor_si256 (a, b); }
298 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot (__m256i a, __m256i b) noexcept { return _mm256_andnot_si256 (a, b); }
299 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not (__m256i a) noexcept { return _mm256_andnot_si256 (a, load (kAllBitsSet)); }
300 static forcedinline __m256i JUCE_VECTOR_CALLTYPE min (__m256i a, __m256i b) noexcept { return _mm256_min_epu8 (a, b); }
301 static forcedinline __m256i JUCE_VECTOR_CALLTYPE max (__m256i a, __m256i b) noexcept { return _mm256_max_epu8 (a, b); }
302 static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal (__m256i a, __m256i b) noexcept { return _mm256_cmpeq_epi8 (a, b); }
303 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan (__m256i a, __m256i b) noexcept { return _mm256_cmpgt_epi8 (ssign (a), ssign (b)); }
304 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256i a, __m256i b) noexcept { return bit_or (greaterThan (a, b), equal (a,b)); }
305 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256i a, __m256i b) noexcept { return (_mm256_movemask_epi8 (equal (a, b)) == -1); }
306 static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd (__m256i a, __m256i b, __m256i c) noexcept { return add (a, mul (b, c)); }
307 static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual (__m256i a, __m256i b) noexcept { return bit_not (equal (a, b)); }
308 static forcedinline uint8_t JUCE_VECTOR_CALLTYPE get (__m256i v, size_t i) noexcept { return SIMDFallbackOps<uint8_t, __m256i>::get (v, i); }
309 static forcedinline __m256i JUCE_VECTOR_CALLTYPE set (__m256i v, size_t i, uint8_t s) noexcept { return SIMDFallbackOps<uint8_t, __m256i>::set (v, i, s); }
310 static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate (__m256i a) noexcept { return a; }
311
312 //==============================================================================
313 static forcedinline uint8_t JUCE_VECTOR_CALLTYPE sum (__m256i a) noexcept
314 {
315 __m256i lo = _mm256_unpacklo_epi8 (a, _mm256_setzero_si256());
316 __m256i hi = _mm256_unpackhi_epi8 (a, _mm256_setzero_si256());
317
318 for (int i = 0; i < 3; ++i)
319 {
320 lo = _mm256_hadd_epi16 (lo, lo);
321 hi = _mm256_hadd_epi16 (hi, hi);
322 }
323
324 #if JUCE_GCC
325 return (uint8_t) ((static_cast<uint32_t> (lo[0]) & 0xffu) +
326 (static_cast<uint32_t> (hi[0]) & 0xffu) +
327 (static_cast<uint32_t> (lo[2]) & 0xffu) +
328 (static_cast<uint32_t> (hi[2]) & 0xffu));
329 #else
330 constexpr int mask = (2 << 0) | (3 << 2) | (0 << 4) | (1 << 6);
331
332 return (uint8_t) ((static_cast<uint32_t> (_mm256_cvtsi256_si32 (lo)) & 0xffu) +
333 (static_cast<uint32_t> (_mm256_cvtsi256_si32 (hi)) & 0xffu) +
334 (static_cast<uint32_t> (_mm256_cvtsi256_si32 (_mm256_permute4x64_epi64 (lo, mask))) & 0xffu) +
335 (static_cast<uint32_t> (_mm256_cvtsi256_si32 (_mm256_permute4x64_epi64 (hi, mask))) & 0xffu));
336 #endif
337 }
338
339 static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul (__m256i a, __m256i b)
340 {
341 // unpack and multiply
342 __m256i even = _mm256_mullo_epi16 (a, b);
343 __m256i odd = _mm256_mullo_epi16 (_mm256_srli_epi16 (a, 8), _mm256_srli_epi16 (b, 8));
344
345 return _mm256_or_si256 (_mm256_slli_epi16 (odd, 8),
346 _mm256_srli_epi16 (_mm256_slli_epi16 (even, 8), 8));
347 }
348};
349
350//==============================================================================
355template <>
356struct SIMDNativeOps<int16_t>
357{
358 //==============================================================================
359 using vSIMDType = __m256i;
360
361 //==============================================================================
362 DECLARE_AVX_SIMD_CONST (int16_t, kAllBitsSet);
363
364 //==============================================================================
365 static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand (int16_t s) noexcept { return _mm256_set1_epi16 (s); }
366 static forcedinline __m256i JUCE_VECTOR_CALLTYPE load (const int16_t* p) noexcept { return _mm256_load_si256 (reinterpret_cast<const __m256i*> (p)); }
367 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256i value, int16_t* dest) noexcept { _mm256_store_si256 (reinterpret_cast<__m256i*> (dest), value); }
368 static forcedinline __m256i JUCE_VECTOR_CALLTYPE add (__m256i a, __m256i b) noexcept { return _mm256_add_epi16 (a, b); }
369 static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub (__m256i a, __m256i b) noexcept { return _mm256_sub_epi16 (a, b); }
370 static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul (__m256i a, __m256i b) noexcept { return _mm256_mullo_epi16 (a, b); }
371 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and (__m256i a, __m256i b) noexcept { return _mm256_and_si256 (a, b); }
372 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or (__m256i a, __m256i b) noexcept { return _mm256_or_si256 (a, b); }
373 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor (__m256i a, __m256i b) noexcept { return _mm256_xor_si256 (a, b); }
374 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot (__m256i a, __m256i b) noexcept { return _mm256_andnot_si256 (a, b); }
375 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not (__m256i a) noexcept { return _mm256_andnot_si256 (a, load (kAllBitsSet)); }
376 static forcedinline __m256i JUCE_VECTOR_CALLTYPE min (__m256i a, __m256i b) noexcept { return _mm256_min_epi16 (a, b); }
377 static forcedinline __m256i JUCE_VECTOR_CALLTYPE max (__m256i a, __m256i b) noexcept { return _mm256_max_epi16 (a, b); }
378 static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal (__m256i a, __m256i b) noexcept { return _mm256_cmpeq_epi16 (a, b); }
379 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan (__m256i a, __m256i b) noexcept { return _mm256_cmpgt_epi16 (a, b); }
380 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256i a, __m256i b) noexcept { return bit_or (greaterThan (a, b), equal (a,b)); }
381 static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd (__m256i a, __m256i b, __m256i c) noexcept { return add (a, mul (b, c)); }
382 static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual (__m256i a, __m256i b) noexcept { return bit_not (equal (a, b)); }
383 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256i a, __m256i b) noexcept { return (_mm256_movemask_epi8 (equal (a, b)) == -1); }
384 static forcedinline int16_t JUCE_VECTOR_CALLTYPE get (__m256i v, size_t i) noexcept { return SIMDFallbackOps<int16_t, __m256i>::get (v, i); }
385 static forcedinline __m256i JUCE_VECTOR_CALLTYPE set (__m256i v, size_t i, int16_t s) noexcept { return SIMDFallbackOps<int16_t, __m256i>::set (v, i, s); }
386 static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate (__m256i a) noexcept { return a; }
387
388 //==============================================================================
389 static forcedinline int16_t JUCE_VECTOR_CALLTYPE sum (__m256i a) noexcept
390 {
391 __m256i tmp = _mm256_hadd_epi16 (a, a);
392 tmp = _mm256_hadd_epi16 (tmp, tmp);
393 tmp = _mm256_hadd_epi16 (tmp, tmp);
394
395 #if JUCE_GCC
396 return (int16_t) ((tmp[0] & 0xffff) + (tmp[2] & 0xffff));
397 #else
398 constexpr int mask = (2 << 0) | (3 << 2) | (0 << 4) | (1 << 6);
399
400 return (int16_t) ((_mm256_cvtsi256_si32 (tmp) & 0xffff) +
401 (_mm256_cvtsi256_si32 (_mm256_permute4x64_epi64 (tmp, mask)) & 0xffff));
402 #endif
403 }
404};
405
406//==============================================================================
411template <>
412struct SIMDNativeOps<uint16_t>
413{
414 //==============================================================================
415 using vSIMDType = __m256i;
416
417 //==============================================================================
418 DECLARE_AVX_SIMD_CONST (uint16_t, kHighBit);
419 DECLARE_AVX_SIMD_CONST (uint16_t, kAllBitsSet);
420
421 //==============================================================================
422 static forcedinline __m256i JUCE_VECTOR_CALLTYPE ssign (__m256i a) noexcept { return _mm256_xor_si256 (a, load (kHighBit)); }
423 static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand (uint16_t s) noexcept { return _mm256_set1_epi16 ((int16_t) s); }
424 static forcedinline __m256i JUCE_VECTOR_CALLTYPE load (const uint16_t* p) noexcept { return _mm256_load_si256 (reinterpret_cast<const __m256i*> (p)); }
425 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256i value, uint16_t* dest) noexcept { _mm256_store_si256 (reinterpret_cast<__m256i*> (dest), value); }
426 static forcedinline __m256i JUCE_VECTOR_CALLTYPE add (__m256i a, __m256i b) noexcept { return _mm256_add_epi16 (a, b); }
427 static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub (__m256i a, __m256i b) noexcept { return _mm256_sub_epi16 (a, b); }
428 static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul (__m256i a, __m256i b) noexcept { return _mm256_mullo_epi16 (a, b); }
429 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and (__m256i a, __m256i b) noexcept { return _mm256_and_si256 (a, b); }
430 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or (__m256i a, __m256i b) noexcept { return _mm256_or_si256 (a, b); }
431 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor (__m256i a, __m256i b) noexcept { return _mm256_xor_si256 (a, b); }
432 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot (__m256i a, __m256i b) noexcept { return _mm256_andnot_si256 (a, b); }
433 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not (__m256i a) noexcept { return _mm256_andnot_si256 (a, load (kAllBitsSet)); }
434 static forcedinline __m256i JUCE_VECTOR_CALLTYPE min (__m256i a, __m256i b) noexcept { return _mm256_min_epu16 (a, b); }
435 static forcedinline __m256i JUCE_VECTOR_CALLTYPE max (__m256i a, __m256i b) noexcept { return _mm256_max_epu16 (a, b); }
436 static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal (__m256i a, __m256i b) noexcept { return _mm256_cmpeq_epi16 (a, b); }
437 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan (__m256i a, __m256i b) noexcept { return _mm256_cmpgt_epi16 (ssign (a), ssign (b)); }
438 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256i a, __m256i b) noexcept { return bit_or (greaterThan (a, b), equal (a,b)); }
439 static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd (__m256i a, __m256i b, __m256i c) noexcept { return add (a, mul (b, c)); }
440 static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual (__m256i a, __m256i b) noexcept { return bit_not (equal (a, b)); }
441 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256i a, __m256i b) noexcept { return (_mm256_movemask_epi8 (equal (a, b)) == -1); }
442 static forcedinline uint16_t JUCE_VECTOR_CALLTYPE get (__m256i v, size_t i) noexcept { return SIMDFallbackOps<uint16_t, __m256i>::get (v, i); }
443 static forcedinline __m256i JUCE_VECTOR_CALLTYPE set (__m256i v, size_t i, uint16_t s) noexcept { return SIMDFallbackOps<uint16_t, __m256i>::set (v, i, s); }
444 static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate (__m256i a) noexcept { return a; }
445
446 //==============================================================================
447 static forcedinline uint16_t JUCE_VECTOR_CALLTYPE sum (__m256i a) noexcept
448 {
449 __m256i tmp = _mm256_hadd_epi16 (a, a);
450 tmp = _mm256_hadd_epi16 (tmp, tmp);
451 tmp = _mm256_hadd_epi16 (tmp, tmp);
452
453 #if JUCE_GCC
454 return (uint16_t) ((static_cast<uint32_t> (tmp[0]) & 0xffffu) +
455 (static_cast<uint32_t> (tmp[2]) & 0xffffu));
456 #else
457 constexpr int mask = (2 << 0) | (3 << 2) | (0 << 4) | (1 << 6);
458
459 return (uint16_t) ((static_cast<uint32_t> (_mm256_cvtsi256_si32 (tmp)) & 0xffffu) +
460 (static_cast<uint32_t> (_mm256_cvtsi256_si32 (_mm256_permute4x64_epi64 (tmp, mask))) & 0xffffu));
461 #endif
462 }
463};
464
465//==============================================================================
470template <>
471struct SIMDNativeOps<int32_t>
472{
473 //==============================================================================
474 using vSIMDType = __m256i;
475
476 //==============================================================================
477 DECLARE_AVX_SIMD_CONST (int32_t, kAllBitsSet);
478
479 //==============================================================================
480 static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand (int32_t s) noexcept { return _mm256_set1_epi32 (s); }
481 static forcedinline __m256i JUCE_VECTOR_CALLTYPE load (const int32_t* p) noexcept { return _mm256_load_si256 (reinterpret_cast<const __m256i*> (p)); }
482 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256i value, int32_t* dest) noexcept { _mm256_store_si256 (reinterpret_cast<__m256i*> (dest), value); }
483 static forcedinline __m256i JUCE_VECTOR_CALLTYPE add (__m256i a, __m256i b) noexcept { return _mm256_add_epi32 (a, b); }
484 static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub (__m256i a, __m256i b) noexcept { return _mm256_sub_epi32 (a, b); }
485 static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul (__m256i a, __m256i b) noexcept { return _mm256_mullo_epi32 (a, b); }
486 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and (__m256i a, __m256i b) noexcept { return _mm256_and_si256 (a, b); }
487 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or (__m256i a, __m256i b) noexcept { return _mm256_or_si256 (a, b); }
488 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor (__m256i a, __m256i b) noexcept { return _mm256_xor_si256 (a, b); }
489 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot (__m256i a, __m256i b) noexcept { return _mm256_andnot_si256 (a, b); }
490 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not (__m256i a) noexcept { return _mm256_andnot_si256 (a, load (kAllBitsSet)); }
491 static forcedinline __m256i JUCE_VECTOR_CALLTYPE min (__m256i a, __m256i b) noexcept { return _mm256_min_epi32 (a, b); }
492 static forcedinline __m256i JUCE_VECTOR_CALLTYPE max (__m256i a, __m256i b) noexcept { return _mm256_max_epi32 (a, b); }
493 static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal (__m256i a, __m256i b) noexcept { return _mm256_cmpeq_epi32 (a, b); }
494 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan (__m256i a, __m256i b) noexcept { return _mm256_cmpgt_epi32 (a, b); }
495 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256i a, __m256i b) noexcept { return bit_or (greaterThan (a, b), equal (a,b)); }
496 static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd (__m256i a, __m256i b, __m256i c) noexcept { return add (a, mul (b, c)); }
497 static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual (__m256i a, __m256i b) noexcept { return bit_not (equal (a, b)); }
498 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256i a, __m256i b) noexcept { return (_mm256_movemask_epi8 (equal (a, b)) == -1); }
499 static forcedinline int32_t JUCE_VECTOR_CALLTYPE get (__m256i v, size_t i) noexcept { return SIMDFallbackOps<int32_t, __m256i>::get (v, i); }
500 static forcedinline __m256i JUCE_VECTOR_CALLTYPE set (__m256i v, size_t i, int32_t s) noexcept { return SIMDFallbackOps<int32_t, __m256i>::set (v, i, s); }
501 static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate (__m256i a) noexcept { return a; }
502
503 //==============================================================================
504 static forcedinline int32_t JUCE_VECTOR_CALLTYPE sum (__m256i a) noexcept
505 {
506 __m256i tmp = _mm256_hadd_epi32 (a, a);
507 tmp = _mm256_hadd_epi32 (tmp, tmp);
508
509 #if JUCE_GCC
510 return (int32_t) (tmp[0] + tmp[2]);
511 #else
512 constexpr int mask = (2 << 0) | (3 << 2) | (0 << 4) | (1 << 6);
513
514 return _mm256_cvtsi256_si32 (tmp) + _mm256_cvtsi256_si32 (_mm256_permute4x64_epi64 (tmp, mask));
515 #endif
516 }
517};
518
519//==============================================================================
524template <>
525struct SIMDNativeOps<uint32_t>
526{
527 //==============================================================================
528 using vSIMDType = __m256i;
529
530 //==============================================================================
531 DECLARE_AVX_SIMD_CONST (uint32_t, kAllBitsSet);
532 DECLARE_AVX_SIMD_CONST (uint32_t, kHighBit);
533
534 //==============================================================================
535 static forcedinline __m256i JUCE_VECTOR_CALLTYPE ssign (__m256i a) noexcept { return _mm256_xor_si256 (a, load (kHighBit)); }
536 static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand (uint32_t s) noexcept { return _mm256_set1_epi32 ((int32_t) s); }
537 static forcedinline __m256i JUCE_VECTOR_CALLTYPE load (const uint32_t* p) noexcept { return _mm256_load_si256 (reinterpret_cast<const __m256i*> (p)); }
538 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256i value, uint32_t* dest) noexcept { _mm256_store_si256 (reinterpret_cast<__m256i*> (dest), value); }
539 static forcedinline __m256i JUCE_VECTOR_CALLTYPE add (__m256i a, __m256i b) noexcept { return _mm256_add_epi32 (a, b); }
540 static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub (__m256i a, __m256i b) noexcept { return _mm256_sub_epi32 (a, b); }
541 static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul (__m256i a, __m256i b) noexcept { return _mm256_mullo_epi32 (a, b); }
542 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and (__m256i a, __m256i b) noexcept { return _mm256_and_si256 (a, b); }
543 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or (__m256i a, __m256i b) noexcept { return _mm256_or_si256 (a, b); }
544 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor (__m256i a, __m256i b) noexcept { return _mm256_xor_si256 (a, b); }
545 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot (__m256i a, __m256i b) noexcept { return _mm256_andnot_si256 (a, b); }
546 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not (__m256i a) noexcept { return _mm256_andnot_si256 (a, load (kAllBitsSet)); }
547 static forcedinline __m256i JUCE_VECTOR_CALLTYPE min (__m256i a, __m256i b) noexcept { return _mm256_min_epu32 (a, b); }
548 static forcedinline __m256i JUCE_VECTOR_CALLTYPE max (__m256i a, __m256i b) noexcept { return _mm256_max_epu32 (a, b); }
549 static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal (__m256i a, __m256i b) noexcept { return _mm256_cmpeq_epi32 (a, b); }
550 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan (__m256i a, __m256i b) noexcept { return _mm256_cmpgt_epi32 (ssign (a), ssign (b)); }
551 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256i a, __m256i b) noexcept { return bit_or (greaterThan (a, b), equal (a,b)); }
552 static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd (__m256i a, __m256i b, __m256i c) noexcept { return add (a, mul (b, c)); }
553 static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual (__m256i a, __m256i b) noexcept { return bit_not (equal (a, b)); }
554 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256i a, __m256i b) noexcept { return (_mm256_movemask_epi8 (equal (a, b)) == -1); }
555 static forcedinline uint32_t JUCE_VECTOR_CALLTYPE get (__m256i v, size_t i) noexcept { return SIMDFallbackOps<uint32_t, __m256i>::get (v, i); }
556 static forcedinline __m256i JUCE_VECTOR_CALLTYPE set (__m256i v, size_t i, uint32_t s) noexcept { return SIMDFallbackOps<uint32_t, __m256i>::set (v, i, s); }
557 static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate (__m256i a) noexcept { return a; }
558
559 //==============================================================================
560 static forcedinline uint32_t JUCE_VECTOR_CALLTYPE sum (__m256i a) noexcept
561 {
562 __m256i tmp = _mm256_hadd_epi32 (a, a);
563 tmp = _mm256_hadd_epi32 (tmp, tmp);
564
565 #if JUCE_GCC
566 return static_cast<uint32_t> (tmp[0]) + static_cast<uint32_t> (tmp[2]);
567 #else
568 constexpr int mask = (2 << 0) | (3 << 2) | (0 << 4) | (1 << 6);
569
570 return static_cast<uint32_t> (_mm256_cvtsi256_si32 (tmp))
571 + static_cast<uint32_t> (_mm256_cvtsi256_si32 (_mm256_permute4x64_epi64 (tmp, mask)));
572 #endif
573 }
574};
575
576//==============================================================================
581template <>
582struct SIMDNativeOps<int64_t>
583{
584 //==============================================================================
585 using vSIMDType = __m256i;
586
587 //==============================================================================
588 DECLARE_AVX_SIMD_CONST (int64_t, kAllBitsSet);
589
590 static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand (int64_t s) noexcept { return _mm256_set1_epi64x ((int64_t) s); }
591 static forcedinline __m256i JUCE_VECTOR_CALLTYPE load (const int64_t* p) noexcept { return _mm256_load_si256 (reinterpret_cast<const __m256i*> (p)); }
592 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256i value, int64_t* dest) noexcept { _mm256_store_si256 (reinterpret_cast<__m256i*> (dest), value); }
593 static forcedinline __m256i JUCE_VECTOR_CALLTYPE add (__m256i a, __m256i b) noexcept { return _mm256_add_epi64 (a, b); }
594 static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub (__m256i a, __m256i b) noexcept { return _mm256_sub_epi64 (a, b); }
595 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and (__m256i a, __m256i b) noexcept { return _mm256_and_si256 (a, b); }
596 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or (__m256i a, __m256i b) noexcept { return _mm256_or_si256 (a, b); }
597 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor (__m256i a, __m256i b) noexcept { return _mm256_xor_si256 (a, b); }
598 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot (__m256i a, __m256i b) noexcept { return _mm256_andnot_si256 (a, b); }
599 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not (__m256i a) noexcept { return _mm256_andnot_si256 (a, load (kAllBitsSet)); }
600 static forcedinline __m256i JUCE_VECTOR_CALLTYPE min (__m256i a, __m256i b) noexcept { __m256i lt = greaterThan (b, a); return bit_or (bit_and (lt, a), bit_andnot (lt, b)); }
601 static forcedinline __m256i JUCE_VECTOR_CALLTYPE max (__m256i a, __m256i b) noexcept { __m256i gt = greaterThan (a, b); return bit_or (bit_and (gt, a), bit_andnot (gt, b)); }
602 static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal (__m256i a, __m256i b) noexcept { return _mm256_cmpeq_epi64 (a, b); }
603 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan (__m256i a, __m256i b) noexcept { return _mm256_cmpgt_epi64 (a, b); }
604 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256i a, __m256i b) noexcept { return bit_or (greaterThan (a, b), equal (a,b)); }
605 static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd (__m256i a, __m256i b, __m256i c) noexcept { return add (a, mul (b, c)); }
606 static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual (__m256i a, __m256i b) noexcept { return bit_not (equal (a, b)); }
607 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256i a, __m256i b) noexcept { return (_mm256_movemask_epi8 (equal (a, b)) == -1); }
608 static forcedinline int64_t JUCE_VECTOR_CALLTYPE get (__m256i v, size_t i) noexcept { return SIMDFallbackOps<int64_t, __m256i>::get (v, i); }
609 static forcedinline __m256i JUCE_VECTOR_CALLTYPE set (__m256i v, size_t i, int64_t s) noexcept { return SIMDFallbackOps<int64_t, __m256i>::set (v, i, s); }
610 static forcedinline int64_t JUCE_VECTOR_CALLTYPE sum (__m256i a) noexcept { return SIMDFallbackOps<int64_t, __m256i>::sum (a); }
611 static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul (__m256i a, __m256i b) noexcept { return SIMDFallbackOps<int64_t, __m256i>::mul (a, b); }
612 static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate (__m256i a) noexcept { return a; }
613};
614
615//==============================================================================
620template <>
621struct SIMDNativeOps<uint64_t>
622{
623 //==============================================================================
624 using vSIMDType = __m256i;
625
626 //==============================================================================
627 DECLARE_AVX_SIMD_CONST (uint64_t, kAllBitsSet);
628 DECLARE_AVX_SIMD_CONST (uint64_t, kHighBit);
629
630 static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand (uint64_t s) noexcept { return _mm256_set1_epi64x ((int64_t) s); }
631 static forcedinline __m256i JUCE_VECTOR_CALLTYPE load (const uint64_t* p) noexcept { return _mm256_load_si256 (reinterpret_cast<const __m256i*> (p)); }
632 static forcedinline void JUCE_VECTOR_CALLTYPE store (__m256i value, uint64_t* dest) noexcept { _mm256_store_si256 (reinterpret_cast<__m256i*> (dest), value); }
633 static forcedinline __m256i JUCE_VECTOR_CALLTYPE ssign (__m256i a) noexcept { return _mm256_xor_si256 (a, load (kHighBit)); }
634 static forcedinline __m256i JUCE_VECTOR_CALLTYPE add (__m256i a, __m256i b) noexcept { return _mm256_add_epi64 (a, b); }
635 static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub (__m256i a, __m256i b) noexcept { return _mm256_sub_epi64 (a, b); }
636 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and (__m256i a, __m256i b) noexcept { return _mm256_and_si256 (a, b); }
637 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or (__m256i a, __m256i b) noexcept { return _mm256_or_si256 (a, b); }
638 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor (__m256i a, __m256i b) noexcept { return _mm256_xor_si256 (a, b); }
639 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot (__m256i a, __m256i b) noexcept { return _mm256_andnot_si256 (a, b); }
640 static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not (__m256i a) noexcept { return _mm256_andnot_si256 (a, load (kAllBitsSet)); }
641 static forcedinline __m256i JUCE_VECTOR_CALLTYPE min (__m256i a, __m256i b) noexcept { __m256i lt = greaterThan (b, a); return bit_or (bit_and (lt, a), bit_andnot (lt, b)); }
642 static forcedinline __m256i JUCE_VECTOR_CALLTYPE max (__m256i a, __m256i b) noexcept { __m256i gt = greaterThan (a, b); return bit_or (bit_and (gt, a), bit_andnot (gt, b)); }
643 static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal (__m256i a, __m256i b) noexcept { return _mm256_cmpeq_epi64 (a, b); }
644 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan (__m256i a, __m256i b) noexcept { return _mm256_cmpgt_epi64 (ssign (a), ssign (b)); }
645 static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual (__m256i a, __m256i b) noexcept { return bit_or (greaterThan (a, b), equal (a,b)); }
646 static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd (__m256i a, __m256i b, __m256i c) noexcept { return add (a, mul (b, c)); }
647 static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual (__m256i a, __m256i b) noexcept { return bit_not (equal (a, b)); }
648 static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual (__m256i a, __m256i b) noexcept { return (_mm256_movemask_epi8 (equal (a, b)) == -1); }
649 static forcedinline uint64_t JUCE_VECTOR_CALLTYPE get (__m256i v, size_t i) noexcept { return SIMDFallbackOps<uint64_t, __m256i>::get (v, i); }
650 static forcedinline __m256i JUCE_VECTOR_CALLTYPE set (__m256i v, size_t i, uint64_t s) noexcept { return SIMDFallbackOps<uint64_t, __m256i>::set (v, i, s); }
651 static forcedinline uint64_t JUCE_VECTOR_CALLTYPE sum (__m256i a) noexcept { return SIMDFallbackOps<uint64_t, __m256i>::sum (a); }
652 static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul (__m256i a, __m256i b) noexcept { return SIMDFallbackOps<uint64_t, __m256i>::mul (a, b); }
653 static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate (__m256i a) noexcept { return a; }
654};
655
656#endif
657
658JUCE_END_IGNORE_WARNINGS_GCC_LIKE
659
660} // namespace dsp
661} // namespace juce
a
uint8_t a
Definition Spc_Cpu.h:141
mask
static const unsigned long mask[]
Definition bitwise.c:31
v
unsigned v[N_MAX]
Definition inflate.c:1584
i
register unsigned i
Definition inflate.c:1575
retval
int retval
Definition inflate.c:947
s
unsigned s
Definition inflate.c:1555
value
static PuglViewHint int value
Definition pugl.h:1708
JUCE_BEGIN_IGNORE_WARNINGS_GCC_LIKE
#define JUCE_BEGIN_IGNORE_WARNINGS_GCC_LIKE(...)
Definition juce_CompilerWarnings.h:181
JUCE_END_IGNORE_WARNINGS_GCC_LIKE
#define JUCE_END_IGNORE_WARNINGS_GCC_LIKE
Definition juce_CompilerWarnings.h:182
forcedinline
#define forcedinline
JUCE_VECTOR_CALLTYPE
#define JUCE_VECTOR_CALLTYPE
Definition juce_dsp.h:100
uint16_t
unsigned short uint16_t
Definition mid.cpp:99
int32_t
int int32_t
Definition mid.cpp:97
uint32_t
unsigned int uint32_t
Definition mid.cpp:100
int16_t
short int16_t
Definition mid.cpp:96
uint8_t
unsigned char uint8_t
Definition mid.cpp:98
int8_t
signed char int8_t
Definition mid.cpp:95
juce::dsp
Definition juce_AudioBlock.h:29
juce
Definition carla_juce.cpp:31
juce::dsp::SIMDFallbackOps::set
static forcedinline vSIMDType set(vSIMDType v, size_t i, ScalarType s) noexcept
Definition juce_fallback_SIMDNativeOps.h:93
juce::dsp::SIMDFallbackOps::sum
static forcedinline ScalarType sum(vSIMDType av) noexcept
Definition juce_fallback_SIMDNativeOps.h:111
juce::dsp::SIMDFallbackOps::mul
static forcedinline vSIMDType mul(vSIMDType a, vSIMDType b) noexcept
Definition juce_fallback_SIMDNativeOps.h:74
juce::dsp::SIMDFallbackOps::get
static forcedinline ScalarType get(vSIMDType v, size_t i) noexcept
Definition juce_fallback_SIMDNativeOps.h:87
juce::dsp::SIMDNativeOps< double >::set
static forcedinline __m256d JUCE_VECTOR_CALLTYPE set(__m256d v, size_t i, double s) noexcept
Definition juce_avx_SIMDNativeOps.h:176
juce::dsp::SIMDNativeOps< double >::bit_notand
static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_notand(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:161
juce::dsp::SIMDNativeOps< double >::vconst
static forcedinline __m256d JUCE_VECTOR_CALLTYPE vconst(const double *a) noexcept
Definition juce_avx_SIMDNativeOps.h:150
juce::dsp::SIMDNativeOps< double >::load
static forcedinline __m256d JUCE_VECTOR_CALLTYPE load(const double *a) noexcept
Definition juce_avx_SIMDNativeOps.h:153
juce::dsp::SIMDNativeOps< double >::oddevensum
static forcedinline __m256d JUCE_VECTOR_CALLTYPE oddevensum(__m256d a) noexcept
Definition juce_avx_SIMDNativeOps.h:174
juce::dsp::SIMDNativeOps< double >::bit_or
static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_or(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:159
juce::dsp::SIMDNativeOps< double >::dupodd
static forcedinline __m256d JUCE_VECTOR_CALLTYPE dupodd(__m256d a) noexcept
Definition juce_avx_SIMDNativeOps.h:172
juce::dsp::SIMDNativeOps< double >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256d value, double *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:154
juce::dsp::SIMDNativeOps< double >::notEqual
static forcedinline __m256d JUCE_VECTOR_CALLTYPE notEqual(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:166
juce::dsp::SIMDNativeOps< double >::get
static forcedinline double JUCE_VECTOR_CALLTYPE get(__m256d v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:175
juce::dsp::SIMDNativeOps< double >::bit_xor
static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_xor(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:160
juce::dsp::SIMDNativeOps< double >::truncate
static forcedinline __m256d JUCE_VECTOR_CALLTYPE truncate(__m256d a) noexcept
Definition juce_avx_SIMDNativeOps.h:177
juce::dsp::SIMDNativeOps< double >::vconst
static forcedinline __m256d JUCE_VECTOR_CALLTYPE vconst(const int64_t *a) noexcept
Definition juce_avx_SIMDNativeOps.h:151
juce::dsp::SIMDNativeOps< double >::vSIMDType
__m256d vSIMDType
Definition juce_avx_SIMDNativeOps.h:142
juce::dsp::SIMDNativeOps< double >::greaterThan
static forcedinline __m256d JUCE_VECTOR_CALLTYPE greaterThan(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:167
juce::dsp::SIMDNativeOps< double >::bit_not
static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_not(__m256d a) noexcept
Definition juce_avx_SIMDNativeOps.h:162
juce::dsp::SIMDNativeOps< double >::sub
static forcedinline __m256d JUCE_VECTOR_CALLTYPE sub(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:156
juce::dsp::SIMDNativeOps< double >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:169
juce::dsp::SIMDNativeOps< double >::dupeven
static forcedinline __m256d JUCE_VECTOR_CALLTYPE dupeven(__m256d a) noexcept
Definition juce_avx_SIMDNativeOps.h:171
juce::dsp::SIMDNativeOps< double >::sum
static forcedinline double JUCE_VECTOR_CALLTYPE sum(__m256d a) noexcept
Definition juce_avx_SIMDNativeOps.h:187
juce::dsp::SIMDNativeOps< double >::add
static forcedinline __m256d JUCE_VECTOR_CALLTYPE add(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:155
juce::dsp::SIMDNativeOps< double >::expand
static forcedinline __m256d JUCE_VECTOR_CALLTYPE expand(double s) noexcept
Definition juce_avx_SIMDNativeOps.h:152
juce::dsp::SIMDNativeOps< double >::greaterThanOrEqual
static forcedinline __m256d JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:168
juce::dsp::SIMDNativeOps< double >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(int64_t, kEvenHighBit)
juce::dsp::SIMDNativeOps< double >::swapevenodd
static forcedinline __m256d JUCE_VECTOR_CALLTYPE swapevenodd(__m256d a) noexcept
Definition juce_avx_SIMDNativeOps.h:173
juce::dsp::SIMDNativeOps< double >::mul
static forcedinline __m256d JUCE_VECTOR_CALLTYPE mul(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:157
juce::dsp::SIMDNativeOps< double >::max
static forcedinline __m256d JUCE_VECTOR_CALLTYPE max(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:164
juce::dsp::SIMDNativeOps< double >::equal
static forcedinline __m256d JUCE_VECTOR_CALLTYPE equal(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:165
juce::dsp::SIMDNativeOps< double >::bit_and
static forcedinline __m256d JUCE_VECTOR_CALLTYPE bit_and(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:158
juce::dsp::SIMDNativeOps< double >::multiplyAdd
static forcedinline __m256d JUCE_VECTOR_CALLTYPE multiplyAdd(__m256d a, __m256d b, __m256d c) noexcept
Definition juce_avx_SIMDNativeOps.h:170
juce::dsp::SIMDNativeOps< double >::min
static forcedinline __m256d JUCE_VECTOR_CALLTYPE min(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:163
juce::dsp::SIMDNativeOps< double >::cmplxmul
static forcedinline __m256d JUCE_VECTOR_CALLTYPE cmplxmul(__m256d a, __m256d b) noexcept
Definition juce_avx_SIMDNativeOps.h:180
juce::dsp::SIMDNativeOps< double >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(int64_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< float >::multiplyAdd
static forcedinline __m256 JUCE_VECTOR_CALLTYPE multiplyAdd(__m256 a, __m256 b, __m256 c) noexcept
Definition juce_avx_SIMDNativeOps.h:97
juce::dsp::SIMDNativeOps< float >::vconst
static forcedinline __m256 JUCE_VECTOR_CALLTYPE vconst(const int32_t *a) noexcept
Definition juce_avx_SIMDNativeOps.h:71
juce::dsp::SIMDNativeOps< float >::bit_or
static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_or(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:79
juce::dsp::SIMDNativeOps< float >::swapevenodd
static forcedinline __m256 JUCE_VECTOR_CALLTYPE swapevenodd(__m256 a) noexcept
Definition juce_avx_SIMDNativeOps.h:92
juce::dsp::SIMDNativeOps< float >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(int32_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< float >::set
static forcedinline __m256 JUCE_VECTOR_CALLTYPE set(__m256 v, size_t i, float s) noexcept
Definition juce_avx_SIMDNativeOps.h:94
juce::dsp::SIMDNativeOps< float >::greaterThan
static forcedinline __m256 JUCE_VECTOR_CALLTYPE greaterThan(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:87
juce::dsp::SIMDNativeOps< float >::cmplxmul
static forcedinline __m256 JUCE_VECTOR_CALLTYPE cmplxmul(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:113
juce::dsp::SIMDNativeOps< float >::bit_not
static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_not(__m256 a) noexcept
Definition juce_avx_SIMDNativeOps.h:82
juce::dsp::SIMDNativeOps< float >::equal
static forcedinline __m256 JUCE_VECTOR_CALLTYPE equal(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:85
juce::dsp::SIMDNativeOps< float >::sum
static forcedinline float JUCE_VECTOR_CALLTYPE sum(__m256 a) noexcept
Definition juce_avx_SIMDNativeOps.h:120
juce::dsp::SIMDNativeOps< float >::expand
static forcedinline __m256 JUCE_VECTOR_CALLTYPE expand(float s) noexcept
Definition juce_avx_SIMDNativeOps.h:72
juce::dsp::SIMDNativeOps< float >::max
static forcedinline __m256 JUCE_VECTOR_CALLTYPE max(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:84
juce::dsp::SIMDNativeOps< float >::dupeven
static forcedinline __m256 JUCE_VECTOR_CALLTYPE dupeven(__m256 a) noexcept
Definition juce_avx_SIMDNativeOps.h:90
juce::dsp::SIMDNativeOps< float >::vconst
static forcedinline __m256 JUCE_VECTOR_CALLTYPE vconst(const float *a) noexcept
Definition juce_avx_SIMDNativeOps.h:70
juce::dsp::SIMDNativeOps< float >::vSIMDType
__m256 vSIMDType
Definition juce_avx_SIMDNativeOps.h:62
juce::dsp::SIMDNativeOps< float >::notEqual
static forcedinline __m256 JUCE_VECTOR_CALLTYPE notEqual(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:86
juce::dsp::SIMDNativeOps< float >::oddevensum
static forcedinline __m256 JUCE_VECTOR_CALLTYPE oddevensum(__m256 a) noexcept
Definition juce_avx_SIMDNativeOps.h:106
juce::dsp::SIMDNativeOps< float >::load
static forcedinline __m256 JUCE_VECTOR_CALLTYPE load(const float *a) noexcept
Definition juce_avx_SIMDNativeOps.h:73
juce::dsp::SIMDNativeOps< float >::mul
static forcedinline __m256 JUCE_VECTOR_CALLTYPE mul(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:77
juce::dsp::SIMDNativeOps< float >::greaterThanOrEqual
static forcedinline __m256 JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:88
juce::dsp::SIMDNativeOps< float >::add
static forcedinline __m256 JUCE_VECTOR_CALLTYPE add(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:75
juce::dsp::SIMDNativeOps< float >::min
static forcedinline __m256 JUCE_VECTOR_CALLTYPE min(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:83
juce::dsp::SIMDNativeOps< float >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256 value, float *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:74
juce::dsp::SIMDNativeOps< float >::get
static forcedinline float JUCE_VECTOR_CALLTYPE get(__m256 v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:93
juce::dsp::SIMDNativeOps< float >::truncate
static forcedinline __m256 JUCE_VECTOR_CALLTYPE truncate(__m256 a) noexcept
Definition juce_avx_SIMDNativeOps.h:95
juce::dsp::SIMDNativeOps< float >::bit_xor
static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_xor(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:80
juce::dsp::SIMDNativeOps< float >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(int32_t, kEvenHighBit)
juce::dsp::SIMDNativeOps< float >::sub
static forcedinline __m256 JUCE_VECTOR_CALLTYPE sub(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:76
juce::dsp::SIMDNativeOps< float >::dupodd
static forcedinline __m256 JUCE_VECTOR_CALLTYPE dupodd(__m256 a) noexcept
Definition juce_avx_SIMDNativeOps.h:91
juce::dsp::SIMDNativeOps< float >::bit_notand
static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_notand(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:81
juce::dsp::SIMDNativeOps< float >::bit_and
static forcedinline __m256 JUCE_VECTOR_CALLTYPE bit_and(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:78
juce::dsp::SIMDNativeOps< float >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256 a, __m256 b) noexcept
Definition juce_avx_SIMDNativeOps.h:89
juce::dsp::SIMDNativeOps< int16_t >::bit_or
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:372
juce::dsp::SIMDNativeOps< int16_t >::sum
static forcedinline int16_t JUCE_VECTOR_CALLTYPE sum(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:389
juce::dsp::SIMDNativeOps< int16_t >::max
static forcedinline __m256i JUCE_VECTOR_CALLTYPE max(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:377
juce::dsp::SIMDNativeOps< int16_t >::bit_andnot
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:374
juce::dsp::SIMDNativeOps< int16_t >::min
static forcedinline __m256i JUCE_VECTOR_CALLTYPE min(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:376
juce::dsp::SIMDNativeOps< int16_t >::set
static forcedinline __m256i JUCE_VECTOR_CALLTYPE set(__m256i v, size_t i, int16_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:385
juce::dsp::SIMDNativeOps< int16_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(int16_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< int16_t >::vSIMDType
__m256i vSIMDType
Definition juce_avx_SIMDNativeOps.h:359
juce::dsp::SIMDNativeOps< int16_t >::notEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:382
juce::dsp::SIMDNativeOps< int16_t >::truncate
static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:386
juce::dsp::SIMDNativeOps< int16_t >::get
static forcedinline int16_t JUCE_VECTOR_CALLTYPE get(__m256i v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:384
juce::dsp::SIMDNativeOps< int16_t >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256i value, int16_t *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:367
juce::dsp::SIMDNativeOps< int16_t >::expand
static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand(int16_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:365
juce::dsp::SIMDNativeOps< int16_t >::add
static forcedinline __m256i JUCE_VECTOR_CALLTYPE add(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:368
juce::dsp::SIMDNativeOps< int16_t >::multiplyAdd
static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd(__m256i a, __m256i b, __m256i c) noexcept
Definition juce_avx_SIMDNativeOps.h:381
juce::dsp::SIMDNativeOps< int16_t >::mul
static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:370
juce::dsp::SIMDNativeOps< int16_t >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:383
juce::dsp::SIMDNativeOps< int16_t >::bit_and
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:371
juce::dsp::SIMDNativeOps< int16_t >::greaterThanOrEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:380
juce::dsp::SIMDNativeOps< int16_t >::load
static forcedinline __m256i JUCE_VECTOR_CALLTYPE load(const int16_t *p) noexcept
Definition juce_avx_SIMDNativeOps.h:366
juce::dsp::SIMDNativeOps< int16_t >::equal
static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:378
juce::dsp::SIMDNativeOps< int16_t >::greaterThan
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:379
juce::dsp::SIMDNativeOps< int16_t >::bit_xor
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:373
juce::dsp::SIMDNativeOps< int16_t >::bit_not
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:375
juce::dsp::SIMDNativeOps< int16_t >::sub
static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:369
juce::dsp::SIMDNativeOps< int32_t >::equal
static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:493
juce::dsp::SIMDNativeOps< int32_t >::bit_xor
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:488
juce::dsp::SIMDNativeOps< int32_t >::truncate
static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:501
juce::dsp::SIMDNativeOps< int32_t >::bit_and
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:486
juce::dsp::SIMDNativeOps< int32_t >::max
static forcedinline __m256i JUCE_VECTOR_CALLTYPE max(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:492
juce::dsp::SIMDNativeOps< int32_t >::get
static forcedinline int32_t JUCE_VECTOR_CALLTYPE get(__m256i v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:499
juce::dsp::SIMDNativeOps< int32_t >::min
static forcedinline __m256i JUCE_VECTOR_CALLTYPE min(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:491
juce::dsp::SIMDNativeOps< int32_t >::bit_andnot
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:489
juce::dsp::SIMDNativeOps< int32_t >::notEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:497
juce::dsp::SIMDNativeOps< int32_t >::greaterThan
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:494
juce::dsp::SIMDNativeOps< int32_t >::vSIMDType
__m256i vSIMDType
Definition juce_avx_SIMDNativeOps.h:474
juce::dsp::SIMDNativeOps< int32_t >::sub
static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:484
juce::dsp::SIMDNativeOps< int32_t >::expand
static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand(int32_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:480
juce::dsp::SIMDNativeOps< int32_t >::mul
static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:485
juce::dsp::SIMDNativeOps< int32_t >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256i value, int32_t *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:482
juce::dsp::SIMDNativeOps< int32_t >::add
static forcedinline __m256i JUCE_VECTOR_CALLTYPE add(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:483
juce::dsp::SIMDNativeOps< int32_t >::greaterThanOrEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:495
juce::dsp::SIMDNativeOps< int32_t >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:498
juce::dsp::SIMDNativeOps< int32_t >::bit_or
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:487
juce::dsp::SIMDNativeOps< int32_t >::load
static forcedinline __m256i JUCE_VECTOR_CALLTYPE load(const int32_t *p) noexcept
Definition juce_avx_SIMDNativeOps.h:481
juce::dsp::SIMDNativeOps< int32_t >::bit_not
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:490
juce::dsp::SIMDNativeOps< int32_t >::multiplyAdd
static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd(__m256i a, __m256i b, __m256i c) noexcept
Definition juce_avx_SIMDNativeOps.h:496
juce::dsp::SIMDNativeOps< int32_t >::set
static forcedinline __m256i JUCE_VECTOR_CALLTYPE set(__m256i v, size_t i, int32_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:500
juce::dsp::SIMDNativeOps< int32_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(int32_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< int32_t >::sum
static forcedinline int32_t JUCE_VECTOR_CALLTYPE sum(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:504
juce::dsp::SIMDNativeOps< int64_t >::sub
static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:594
juce::dsp::SIMDNativeOps< int64_t >::greaterThan
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:603
juce::dsp::SIMDNativeOps< int64_t >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:607
juce::dsp::SIMDNativeOps< int64_t >::load
static forcedinline __m256i JUCE_VECTOR_CALLTYPE load(const int64_t *p) noexcept
Definition juce_avx_SIMDNativeOps.h:591
juce::dsp::SIMDNativeOps< int64_t >::max
static forcedinline __m256i JUCE_VECTOR_CALLTYPE max(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:601
juce::dsp::SIMDNativeOps< int64_t >::bit_not
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:599
juce::dsp::SIMDNativeOps< int64_t >::notEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:606
juce::dsp::SIMDNativeOps< int64_t >::greaterThanOrEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:604
juce::dsp::SIMDNativeOps< int64_t >::bit_and
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:595
juce::dsp::SIMDNativeOps< int64_t >::expand
static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand(int64_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:590
juce::dsp::SIMDNativeOps< int64_t >::bit_xor
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:597
juce::dsp::SIMDNativeOps< int64_t >::sum
static forcedinline int64_t JUCE_VECTOR_CALLTYPE sum(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:610
juce::dsp::SIMDNativeOps< int64_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(int64_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< int64_t >::set
static forcedinline __m256i JUCE_VECTOR_CALLTYPE set(__m256i v, size_t i, int64_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:609
juce::dsp::SIMDNativeOps< int64_t >::multiplyAdd
static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd(__m256i a, __m256i b, __m256i c) noexcept
Definition juce_avx_SIMDNativeOps.h:605
juce::dsp::SIMDNativeOps< int64_t >::min
static forcedinline __m256i JUCE_VECTOR_CALLTYPE min(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:600
juce::dsp::SIMDNativeOps< int64_t >::equal
static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:602
juce::dsp::SIMDNativeOps< int64_t >::mul
static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:611
juce::dsp::SIMDNativeOps< int64_t >::bit_or
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:596
juce::dsp::SIMDNativeOps< int64_t >::truncate
static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:612
juce::dsp::SIMDNativeOps< int64_t >::get
static forcedinline int64_t JUCE_VECTOR_CALLTYPE get(__m256i v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:608
juce::dsp::SIMDNativeOps< int64_t >::vSIMDType
__m256i vSIMDType
Definition juce_avx_SIMDNativeOps.h:585
juce::dsp::SIMDNativeOps< int64_t >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256i value, int64_t *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:592
juce::dsp::SIMDNativeOps< int64_t >::bit_andnot
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:598
juce::dsp::SIMDNativeOps< int64_t >::add
static forcedinline __m256i JUCE_VECTOR_CALLTYPE add(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:593
juce::dsp::SIMDNativeOps< int8_t >::expand
static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand(int8_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:214
juce::dsp::SIMDNativeOps< int8_t >::sub
static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:218
juce::dsp::SIMDNativeOps< int8_t >::bit_or
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:220
juce::dsp::SIMDNativeOps< int8_t >::max
static forcedinline __m256i JUCE_VECTOR_CALLTYPE max(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:225
juce::dsp::SIMDNativeOps< int8_t >::greaterThanOrEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:228
juce::dsp::SIMDNativeOps< int8_t >::sum
static forcedinline int8_t JUCE_VECTOR_CALLTYPE sum(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:237
juce::dsp::SIMDNativeOps< int8_t >::notEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:231
juce::dsp::SIMDNativeOps< int8_t >::get
static forcedinline int8_t JUCE_VECTOR_CALLTYPE get(__m256i v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:232
juce::dsp::SIMDNativeOps< int8_t >::bit_xor
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:221
juce::dsp::SIMDNativeOps< int8_t >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256i value, int8_t *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:216
juce::dsp::SIMDNativeOps< int8_t >::mul
static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul(__m256i a, __m256i b)
Definition juce_avx_SIMDNativeOps.h:263
juce::dsp::SIMDNativeOps< int8_t >::min
static forcedinline __m256i JUCE_VECTOR_CALLTYPE min(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:224
juce::dsp::SIMDNativeOps< int8_t >::load
static forcedinline __m256i JUCE_VECTOR_CALLTYPE load(const int8_t *p) noexcept
Definition juce_avx_SIMDNativeOps.h:215
juce::dsp::SIMDNativeOps< int8_t >::bit_and
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:219
juce::dsp::SIMDNativeOps< int8_t >::equal
static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:226
juce::dsp::SIMDNativeOps< int8_t >::add
static forcedinline __m256i JUCE_VECTOR_CALLTYPE add(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:217
juce::dsp::SIMDNativeOps< int8_t >::bit_andnot
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:222
juce::dsp::SIMDNativeOps< int8_t >::bit_not
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:223
juce::dsp::SIMDNativeOps< int8_t >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:229
juce::dsp::SIMDNativeOps< int8_t >::vSIMDType
__m256i vSIMDType
Definition juce_avx_SIMDNativeOps.h:209
juce::dsp::SIMDNativeOps< int8_t >::greaterThan
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:227
juce::dsp::SIMDNativeOps< int8_t >::truncate
static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:234
juce::dsp::SIMDNativeOps< int8_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(int8_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< int8_t >::set
static forcedinline __m256i JUCE_VECTOR_CALLTYPE set(__m256i v, size_t i, int8_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:233
juce::dsp::SIMDNativeOps< int8_t >::multiplyAdd
static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd(__m256i a, __m256i b, __m256i c) noexcept
Definition juce_avx_SIMDNativeOps.h:230
juce::dsp::SIMDNativeOps< uint16_t >::mul
static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:428
juce::dsp::SIMDNativeOps< uint16_t >::bit_and
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:429
juce::dsp::SIMDNativeOps< uint16_t >::bit_or
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:430
juce::dsp::SIMDNativeOps< uint16_t >::notEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:440
juce::dsp::SIMDNativeOps< uint16_t >::equal
static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:436
juce::dsp::SIMDNativeOps< uint16_t >::greaterThanOrEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:438
juce::dsp::SIMDNativeOps< uint16_t >::sub
static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:427
juce::dsp::SIMDNativeOps< uint16_t >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256i value, uint16_t *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:425
juce::dsp::SIMDNativeOps< uint16_t >::truncate
static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:444
juce::dsp::SIMDNativeOps< uint16_t >::set
static forcedinline __m256i JUCE_VECTOR_CALLTYPE set(__m256i v, size_t i, uint16_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:443
juce::dsp::SIMDNativeOps< uint16_t >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:441
juce::dsp::SIMDNativeOps< uint16_t >::bit_xor
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:431
juce::dsp::SIMDNativeOps< uint16_t >::vSIMDType
__m256i vSIMDType
Definition juce_avx_SIMDNativeOps.h:415
juce::dsp::SIMDNativeOps< uint16_t >::get
static forcedinline uint16_t JUCE_VECTOR_CALLTYPE get(__m256i v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:442
juce::dsp::SIMDNativeOps< uint16_t >::sum
static forcedinline uint16_t JUCE_VECTOR_CALLTYPE sum(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:447
juce::dsp::SIMDNativeOps< uint16_t >::greaterThan
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:437
juce::dsp::SIMDNativeOps< uint16_t >::max
static forcedinline __m256i JUCE_VECTOR_CALLTYPE max(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:435
juce::dsp::SIMDNativeOps< uint16_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(uint16_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< uint16_t >::add
static forcedinline __m256i JUCE_VECTOR_CALLTYPE add(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:426
juce::dsp::SIMDNativeOps< uint16_t >::ssign
static forcedinline __m256i JUCE_VECTOR_CALLTYPE ssign(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:422
juce::dsp::SIMDNativeOps< uint16_t >::min
static forcedinline __m256i JUCE_VECTOR_CALLTYPE min(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:434
juce::dsp::SIMDNativeOps< uint16_t >::bit_andnot
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:432
juce::dsp::SIMDNativeOps< uint16_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(uint16_t, kHighBit)
juce::dsp::SIMDNativeOps< uint16_t >::load
static forcedinline __m256i JUCE_VECTOR_CALLTYPE load(const uint16_t *p) noexcept
Definition juce_avx_SIMDNativeOps.h:424
juce::dsp::SIMDNativeOps< uint16_t >::multiplyAdd
static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd(__m256i a, __m256i b, __m256i c) noexcept
Definition juce_avx_SIMDNativeOps.h:439
juce::dsp::SIMDNativeOps< uint16_t >::expand
static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand(uint16_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:423
juce::dsp::SIMDNativeOps< uint16_t >::bit_not
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:433
juce::dsp::SIMDNativeOps< uint32_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(uint32_t, kHighBit)
juce::dsp::SIMDNativeOps< uint32_t >::bit_xor
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:544
juce::dsp::SIMDNativeOps< uint32_t >::bit_or
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:543
juce::dsp::SIMDNativeOps< uint32_t >::get
static forcedinline uint32_t JUCE_VECTOR_CALLTYPE get(__m256i v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:555
juce::dsp::SIMDNativeOps< uint32_t >::ssign
static forcedinline __m256i JUCE_VECTOR_CALLTYPE ssign(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:535
juce::dsp::SIMDNativeOps< uint32_t >::add
static forcedinline __m256i JUCE_VECTOR_CALLTYPE add(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:539
juce::dsp::SIMDNativeOps< uint32_t >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256i value, uint32_t *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:538
juce::dsp::SIMDNativeOps< uint32_t >::notEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:553
juce::dsp::SIMDNativeOps< uint32_t >::bit_and
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:542
juce::dsp::SIMDNativeOps< uint32_t >::load
static forcedinline __m256i JUCE_VECTOR_CALLTYPE load(const uint32_t *p) noexcept
Definition juce_avx_SIMDNativeOps.h:537
juce::dsp::SIMDNativeOps< uint32_t >::bit_andnot
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:545
juce::dsp::SIMDNativeOps< uint32_t >::greaterThan
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:550
juce::dsp::SIMDNativeOps< uint32_t >::greaterThanOrEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:551
juce::dsp::SIMDNativeOps< uint32_t >::multiplyAdd
static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd(__m256i a, __m256i b, __m256i c) noexcept
Definition juce_avx_SIMDNativeOps.h:552
juce::dsp::SIMDNativeOps< uint32_t >::max
static forcedinline __m256i JUCE_VECTOR_CALLTYPE max(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:548
juce::dsp::SIMDNativeOps< uint32_t >::mul
static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:541
juce::dsp::SIMDNativeOps< uint32_t >::bit_not
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:546
juce::dsp::SIMDNativeOps< uint32_t >::truncate
static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:557
juce::dsp::SIMDNativeOps< uint32_t >::sub
static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:540
juce::dsp::SIMDNativeOps< uint32_t >::min
static forcedinline __m256i JUCE_VECTOR_CALLTYPE min(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:547
juce::dsp::SIMDNativeOps< uint32_t >::sum
static forcedinline uint32_t JUCE_VECTOR_CALLTYPE sum(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:560
juce::dsp::SIMDNativeOps< uint32_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(uint32_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< uint32_t >::equal
static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:549
juce::dsp::SIMDNativeOps< uint32_t >::set
static forcedinline __m256i JUCE_VECTOR_CALLTYPE set(__m256i v, size_t i, uint32_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:556
juce::dsp::SIMDNativeOps< uint32_t >::vSIMDType
__m256i vSIMDType
Definition juce_avx_SIMDNativeOps.h:528
juce::dsp::SIMDNativeOps< uint32_t >::expand
static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand(uint32_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:536
juce::dsp::SIMDNativeOps< uint32_t >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:554
juce::dsp::SIMDNativeOps< uint64_t >::set
static forcedinline __m256i JUCE_VECTOR_CALLTYPE set(__m256i v, size_t i, uint64_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:650
juce::dsp::SIMDNativeOps< uint64_t >::bit_xor
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:638
juce::dsp::SIMDNativeOps< uint64_t >::get
static forcedinline uint64_t JUCE_VECTOR_CALLTYPE get(__m256i v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:649
juce::dsp::SIMDNativeOps< uint64_t >::mul
static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:652
juce::dsp::SIMDNativeOps< uint64_t >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:648
juce::dsp::SIMDNativeOps< uint64_t >::bit_or
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:637
juce::dsp::SIMDNativeOps< uint64_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(uint64_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< uint64_t >::notEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:647
juce::dsp::SIMDNativeOps< uint64_t >::vSIMDType
__m256i vSIMDType
Definition juce_avx_SIMDNativeOps.h:624
juce::dsp::SIMDNativeOps< uint64_t >::min
static forcedinline __m256i JUCE_VECTOR_CALLTYPE min(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:641
juce::dsp::SIMDNativeOps< uint64_t >::multiplyAdd
static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd(__m256i a, __m256i b, __m256i c) noexcept
Definition juce_avx_SIMDNativeOps.h:646
juce::dsp::SIMDNativeOps< uint64_t >::greaterThan
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:644
juce::dsp::SIMDNativeOps< uint64_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(uint64_t, kHighBit)
juce::dsp::SIMDNativeOps< uint64_t >::bit_andnot
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:639
juce::dsp::SIMDNativeOps< uint64_t >::equal
static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:643
juce::dsp::SIMDNativeOps< uint64_t >::load
static forcedinline __m256i JUCE_VECTOR_CALLTYPE load(const uint64_t *p) noexcept
Definition juce_avx_SIMDNativeOps.h:631
juce::dsp::SIMDNativeOps< uint64_t >::ssign
static forcedinline __m256i JUCE_VECTOR_CALLTYPE ssign(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:633
juce::dsp::SIMDNativeOps< uint64_t >::greaterThanOrEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:645
juce::dsp::SIMDNativeOps< uint64_t >::truncate
static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:653
juce::dsp::SIMDNativeOps< uint64_t >::max
static forcedinline __m256i JUCE_VECTOR_CALLTYPE max(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:642
juce::dsp::SIMDNativeOps< uint64_t >::expand
static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand(uint64_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:630
juce::dsp::SIMDNativeOps< uint64_t >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256i value, uint64_t *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:632
juce::dsp::SIMDNativeOps< uint64_t >::sub
static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:635
juce::dsp::SIMDNativeOps< uint64_t >::bit_and
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:636
juce::dsp::SIMDNativeOps< uint64_t >::bit_not
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:640
juce::dsp::SIMDNativeOps< uint64_t >::add
static forcedinline __m256i JUCE_VECTOR_CALLTYPE add(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:634
juce::dsp::SIMDNativeOps< uint64_t >::sum
static forcedinline uint64_t JUCE_VECTOR_CALLTYPE sum(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:651
juce::dsp::SIMDNativeOps< uint8_t >::greaterThanOrEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThanOrEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:304
juce::dsp::SIMDNativeOps< uint8_t >::get
static forcedinline uint8_t JUCE_VECTOR_CALLTYPE get(__m256i v, size_t i) noexcept
Definition juce_avx_SIMDNativeOps.h:308
juce::dsp::SIMDNativeOps< uint8_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(uint8_t, kHighBit)
juce::dsp::SIMDNativeOps< uint8_t >::set
static forcedinline __m256i JUCE_VECTOR_CALLTYPE set(__m256i v, size_t i, uint8_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:309
juce::dsp::SIMDNativeOps< uint8_t >::sum
static forcedinline uint8_t JUCE_VECTOR_CALLTYPE sum(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:313
juce::dsp::SIMDNativeOps< uint8_t >::bit_andnot
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_andnot(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:298
juce::dsp::SIMDNativeOps< uint8_t >::min
static forcedinline __m256i JUCE_VECTOR_CALLTYPE min(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:300
juce::dsp::SIMDNativeOps< uint8_t >::bit_xor
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_xor(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:297
juce::dsp::SIMDNativeOps< uint8_t >::add
static forcedinline __m256i JUCE_VECTOR_CALLTYPE add(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:293
juce::dsp::SIMDNativeOps< uint8_t >::allEqual
static forcedinline bool JUCE_VECTOR_CALLTYPE allEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:305
juce::dsp::SIMDNativeOps< uint8_t >::ssign
static forcedinline __m256i JUCE_VECTOR_CALLTYPE ssign(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:289
juce::dsp::SIMDNativeOps< uint8_t >::vSIMDType
__m256i vSIMDType
Definition juce_avx_SIMDNativeOps.h:283
juce::dsp::SIMDNativeOps< uint8_t >::store
static forcedinline void JUCE_VECTOR_CALLTYPE store(__m256i value, uint8_t *dest) noexcept
Definition juce_avx_SIMDNativeOps.h:292
juce::dsp::SIMDNativeOps< uint8_t >::bit_not
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_not(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:299
juce::dsp::SIMDNativeOps< uint8_t >::sub
static forcedinline __m256i JUCE_VECTOR_CALLTYPE sub(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:294
juce::dsp::SIMDNativeOps< uint8_t >::mul
static forcedinline __m256i JUCE_VECTOR_CALLTYPE mul(__m256i a, __m256i b)
Definition juce_avx_SIMDNativeOps.h:339
juce::dsp::SIMDNativeOps< uint8_t >::truncate
static forcedinline __m256i JUCE_VECTOR_CALLTYPE truncate(__m256i a) noexcept
Definition juce_avx_SIMDNativeOps.h:310
juce::dsp::SIMDNativeOps< uint8_t >::equal
static forcedinline __m256i JUCE_VECTOR_CALLTYPE equal(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:302
juce::dsp::SIMDNativeOps< uint8_t >::bit_and
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_and(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:295
juce::dsp::SIMDNativeOps< uint8_t >::max
static forcedinline __m256i JUCE_VECTOR_CALLTYPE max(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:301
juce::dsp::SIMDNativeOps< uint8_t >::multiplyAdd
static forcedinline __m256i JUCE_VECTOR_CALLTYPE multiplyAdd(__m256i a, __m256i b, __m256i c) noexcept
Definition juce_avx_SIMDNativeOps.h:306
juce::dsp::SIMDNativeOps< uint8_t >::notEqual
static forcedinline __m256i JUCE_VECTOR_CALLTYPE notEqual(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:307
juce::dsp::SIMDNativeOps< uint8_t >::expand
static forcedinline __m256i JUCE_VECTOR_CALLTYPE expand(uint8_t s) noexcept
Definition juce_avx_SIMDNativeOps.h:290
juce::dsp::SIMDNativeOps< uint8_t >::DECLARE_AVX_SIMD_CONST
DECLARE_AVX_SIMD_CONST(uint8_t, kAllBitsSet)
juce::dsp::SIMDNativeOps< uint8_t >::load
static forcedinline __m256i JUCE_VECTOR_CALLTYPE load(const uint8_t *p) noexcept
Definition juce_avx_SIMDNativeOps.h:291
juce::dsp::SIMDNativeOps< uint8_t >::bit_or
static forcedinline __m256i JUCE_VECTOR_CALLTYPE bit_or(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:296
juce::dsp::SIMDNativeOps< uint8_t >::greaterThan
static forcedinline __m256i JUCE_VECTOR_CALLTYPE greaterThan(__m256i a, __m256i b) noexcept
Definition juce_avx_SIMDNativeOps.h:303
juce::dsp::SIMDNativeOps
Definition juce_avx_SIMDNativeOps.h:52
p
uch * p
Definition crypt.c:594
c
return c
Definition crypt.c:175
b
b
Definition crypt.c:628
Generated on for LMMS by doxygen 1.16.1