Coverage Report

Created: 2025-11-16 07:20

next uncovered line (L), next uncovered region (R), next uncovered branch (B)
/src/libvpx/vpx_dsp/x86/variance_avx2.c
Line
Count
Source
1
/*
2
 *  Copyright (c) 2012 The WebM project authors. All Rights Reserved.
3
 *
4
 *  Use of this source code is governed by a BSD-style license
5
 *  that can be found in the LICENSE file in the root of the source
6
 *  tree. An additional intellectual property rights grant can be found
7
 *  in the file PATENTS.  All contributing project authors may
8
 *  be found in the AUTHORS file in the root of the source tree.
9
 */
10
11
#include <immintrin.h>  // AVX2
12
13
#include "./vpx_dsp_rtcd.h"
14
15
/* clang-format off */
16
DECLARE_ALIGNED(32, static const uint8_t, bilinear_filters_avx2[512]) = {
17
  16, 0,  16, 0,  16, 0,  16, 0,  16, 0,  16, 0,  16, 0,  16, 0,
18
  16, 0,  16, 0,  16, 0,  16, 0,  16, 0,  16, 0,  16, 0,  16, 0,
19
  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,
20
  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,
21
  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,
22
  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,
23
  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,
24
  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,
25
  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,
26
  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,  8,
27
  6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10,
28
  6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10, 6,  10,
29
  4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12,
30
  4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12, 4,  12,
31
  2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14,
32
  2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14, 2,  14,
33
};
34
35
DECLARE_ALIGNED(32, static const int8_t, adjacent_sub_avx2[32]) = {
36
  1, -1,  1, -1,  1, -1,  1, -1,  1, -1,  1, -1,  1, -1,  1, -1,
37
  1, -1,  1, -1,  1, -1,  1, -1,  1, -1,  1, -1,  1, -1,  1, -1
38
};
39
/* clang-format on */
40
41
static INLINE void variance_kernel_avx2(const __m256i src, const __m256i ref,
42
                                        __m256i *const sse,
43
943M
                                        __m256i *const sum) {
44
943M
  const __m256i adj_sub = _mm256_load_si256((__m256i const *)adjacent_sub_avx2);
45
46
  // unpack into pairs of source and reference values
47
943M
  const __m256i src_ref0 = _mm256_unpacklo_epi8(src, ref);
48
943M
  const __m256i src_ref1 = _mm256_unpackhi_epi8(src, ref);
49
50
  // subtract adjacent elements using src*1 + ref*-1
51
943M
  const __m256i diff0 = _mm256_maddubs_epi16(src_ref0, adj_sub);
52
943M
  const __m256i diff1 = _mm256_maddubs_epi16(src_ref1, adj_sub);
53
943M
  const __m256i madd0 = _mm256_madd_epi16(diff0, diff0);
54
943M
  const __m256i madd1 = _mm256_madd_epi16(diff1, diff1);
55
56
  // add to the running totals
57
943M
  *sum = _mm256_add_epi16(*sum, _mm256_add_epi16(diff0, diff1));
58
943M
  *sse = _mm256_add_epi32(*sse, _mm256_add_epi32(madd0, madd1));
59
943M
}
60
61
static INLINE void variance_final_from_32bit_sum_avx2(__m256i vsse,
62
                                                      __m128i vsum,
63
                                                      unsigned int *const sse,
64
245M
                                                      int *const sum) {
65
  // extract the low lane and add it to the high lane
66
245M
  const __m128i sse_reg_128 = _mm_add_epi32(_mm256_castsi256_si128(vsse),
67
245M
                                            _mm256_extractf128_si256(vsse, 1));
68
69
  // unpack sse and sum registers and add
70
245M
  const __m128i sse_sum_lo = _mm_unpacklo_epi32(sse_reg_128, vsum);
71
245M
  const __m128i sse_sum_hi = _mm_unpackhi_epi32(sse_reg_128, vsum);
72
245M
  const __m128i sse_sum = _mm_add_epi32(sse_sum_lo, sse_sum_hi);
73
74
  // perform the final summation and extract the results
75
245M
  const __m128i res = _mm_add_epi32(sse_sum, _mm_srli_si128(sse_sum, 8));
76
245M
  *((int *)sse) = _mm_cvtsi128_si32(res);
77
245M
  *((int *)sum) = _mm_extract_epi32(res, 1);
78
245M
}
79
80
static INLINE void variance_final_from_16bit_sum_avx2(__m256i vsse,
81
                                                      __m256i vsum,
82
                                                      unsigned int *const sse,
83
236M
                                                      int *const sum) {
84
  // extract the low lane and add it to the high lane
85
236M
  const __m128i sum_reg_128 = _mm_add_epi16(_mm256_castsi256_si128(vsum),
86
236M
                                            _mm256_extractf128_si256(vsum, 1));
87
236M
  const __m128i sum_reg_64 =
88
236M
      _mm_add_epi16(sum_reg_128, _mm_srli_si128(sum_reg_128, 8));
89
236M
  const __m128i sum_int32 = _mm_cvtepi16_epi32(sum_reg_64);
90
91
236M
  variance_final_from_32bit_sum_avx2(vsse, sum_int32, sse, sum);
92
236M
}
93
94
2.28M
static INLINE __m256i sum_to_32bit_avx2(const __m256i sum) {
95
2.28M
  const __m256i sum_lo = _mm256_cvtepi16_epi32(_mm256_castsi256_si128(sum));
96
2.28M
  const __m256i sum_hi =
97
2.28M
      _mm256_cvtepi16_epi32(_mm256_extractf128_si256(sum, 1));
98
2.28M
  return _mm256_add_epi32(sum_lo, sum_hi);
99
2.28M
}
100
101
static INLINE void variance8_kernel_avx2(
102
    const uint8_t *const src, const int src_stride, const uint8_t *const ref,
103
681M
    const int ref_stride, __m256i *const sse, __m256i *const sum) {
104
681M
  __m128i src0, src1, ref0, ref1;
105
681M
  __m256i ss, rr, diff;
106
107
  // 0 0 0.... 0 s07 s06 s05 s04 s03 s02 s01 s00
108
681M
  src0 = _mm_loadl_epi64((const __m128i *)(src + 0 * src_stride));
109
110
  // 0 0 0.... 0 s17 s16 s15 s14 s13 s12 s11 s10
111
681M
  src1 = _mm_loadl_epi64((const __m128i *)(src + 1 * src_stride));
112
113
  // s17 s16...s11 s10 s07 s06...s01 s00 (8bit)
114
681M
  src0 = _mm_unpacklo_epi64(src0, src1);
115
116
  // s17 s16...s11 s10 s07 s06...s01 s00 (16 bit)
117
681M
  ss = _mm256_cvtepu8_epi16(src0);
118
119
  // 0 0 0.... 0 r07 r06 r05 r04 r03 r02 r01 r00
120
681M
  ref0 = _mm_loadl_epi64((const __m128i *)(ref + 0 * ref_stride));
121
122
  // 0 0 0.... 0 r17 r16 0 r15 0 r14 0 r13 0 r12 0 r11 0 r10
123
681M
  ref1 = _mm_loadl_epi64((const __m128i *)(ref + 1 * ref_stride));
124
125
  // r17 r16...r11 r10 r07 r06...r01 r00 (8 bit)
126
681M
  ref0 = _mm_unpacklo_epi64(ref0, ref1);
127
128
  // r17 r16...r11 r10 r07 r06...r01 r00 (16 bit)
129
681M
  rr = _mm256_cvtepu8_epi16(ref0);
130
131
681M
  diff = _mm256_sub_epi16(ss, rr);
132
681M
  *sse = _mm256_add_epi32(*sse, _mm256_madd_epi16(diff, diff));
133
681M
  *sum = _mm256_add_epi16(*sum, diff);
134
681M
}
135
136
static INLINE void variance16_kernel_avx2(
137
    const uint8_t *const src, const int src_stride, const uint8_t *const ref,
138
514M
    const int ref_stride, __m256i *const sse, __m256i *const sum) {
139
514M
  const __m128i s0 = _mm_loadu_si128((__m128i const *)(src + 0 * src_stride));
140
514M
  const __m128i s1 = _mm_loadu_si128((__m128i const *)(src + 1 * src_stride));
141
514M
  const __m128i r0 = _mm_loadu_si128((__m128i const *)(ref + 0 * ref_stride));
142
514M
  const __m128i r1 = _mm_loadu_si128((__m128i const *)(ref + 1 * ref_stride));
143
514M
  const __m256i s = _mm256_inserti128_si256(_mm256_castsi128_si256(s0), s1, 1);
144
514M
  const __m256i r = _mm256_inserti128_si256(_mm256_castsi128_si256(r0), r1, 1);
145
514M
  variance_kernel_avx2(s, r, sse, sum);
146
514M
}
147
148
static INLINE void variance32_kernel_avx2(const uint8_t *const src,
149
                                          const uint8_t *const ref,
150
                                          __m256i *const sse,
151
429M
                                          __m256i *const sum) {
152
429M
  const __m256i s = _mm256_loadu_si256((__m256i const *)(src));
153
429M
  const __m256i r = _mm256_loadu_si256((__m256i const *)(ref));
154
429M
  variance_kernel_avx2(s, r, sse, sum);
155
429M
}
156
157
static INLINE void variance8_avx2(const uint8_t *src, const int src_stride,
158
                                  const uint8_t *ref, const int ref_stride,
159
                                  const int h, __m256i *const vsse,
160
167M
                                  __m256i *const vsum) {
161
167M
  int i;
162
167M
  *vsum = _mm256_setzero_si256();
163
167M
  *vsse = _mm256_setzero_si256();
164
165
848M
  for (i = 0; i < h; i += 2) {
166
681M
    variance8_kernel_avx2(src, src_stride, ref, ref_stride, vsse, vsum);
167
681M
    src += 2 * src_stride;
168
681M
    ref += 2 * ref_stride;
169
681M
  }
170
167M
}
171
172
static INLINE void variance16_avx2(const uint8_t *src, const int src_stride,
173
                                   const uint8_t *ref, const int ref_stride,
174
                                   const int h, __m256i *const vsse,
175
66.5M
                                   __m256i *const vsum) {
176
66.5M
  int i;
177
66.5M
  *vsum = _mm256_setzero_si256();
178
66.5M
  *vsse = _mm256_setzero_si256();
179
180
580M
  for (i = 0; i < h; i += 2) {
181
514M
    variance16_kernel_avx2(src, src_stride, ref, ref_stride, vsse, vsum);
182
514M
    src += 2 * src_stride;
183
514M
    ref += 2 * ref_stride;
184
514M
  }
185
66.5M
}
186
187
static INLINE void variance32_avx2(const uint8_t *src, const int src_stride,
188
                                   const uint8_t *ref, const int ref_stride,
189
                                   const int h, __m256i *const vsse,
190
10.2M
                                   __m256i *const vsum) {
191
10.2M
  int i;
192
10.2M
  *vsum = _mm256_setzero_si256();
193
10.2M
  *vsse = _mm256_setzero_si256();
194
195
317M
  for (i = 0; i < h; i++) {
196
307M
    variance32_kernel_avx2(src, ref, vsse, vsum);
197
307M
    src += src_stride;
198
307M
    ref += ref_stride;
199
307M
  }
200
10.2M
}
201
202
static INLINE void variance64_avx2(const uint8_t *src, const int src_stride,
203
                                   const uint8_t *ref, const int ref_stride,
204
                                   const int h, __m256i *const vsse,
205
1.90M
                                   __m256i *const vsum) {
206
1.90M
  int i;
207
1.90M
  *vsum = _mm256_setzero_si256();
208
209
63.0M
  for (i = 0; i < h; i++) {
210
61.1M
    variance32_kernel_avx2(src + 0, ref + 0, vsse, vsum);
211
61.1M
    variance32_kernel_avx2(src + 32, ref + 32, vsse, vsum);
212
61.1M
    src += src_stride;
213
61.1M
    ref += ref_stride;
214
61.1M
  }
215
1.90M
}
216
217
void vpx_get16x16var_avx2(const uint8_t *src_ptr, int src_stride,
218
                          const uint8_t *ref_ptr, int ref_stride,
219
0
                          unsigned int *sse, int *sum) {
220
0
  __m256i vsse, vsum;
221
0
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
222
0
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, sum);
223
0
}
224
225
#define FILTER_SRC(filter)                               \
226
  /* filter the source */                                \
227
85.8M
  exp_src_lo = _mm256_maddubs_epi16(exp_src_lo, filter); \
228
85.8M
  exp_src_hi = _mm256_maddubs_epi16(exp_src_hi, filter); \
229
85.8M
                                                         \
230
85.8M
  /* add 8 to source */                                  \
231
85.8M
  exp_src_lo = _mm256_add_epi16(exp_src_lo, pw8);        \
232
85.8M
  exp_src_hi = _mm256_add_epi16(exp_src_hi, pw8);        \
233
85.8M
                                                         \
234
85.8M
  /* divide source by 16 */                              \
235
85.8M
  exp_src_lo = _mm256_srai_epi16(exp_src_lo, 4);         \
236
85.8M
  exp_src_hi = _mm256_srai_epi16(exp_src_hi, 4);
237
238
#define CALC_SUM_SSE_INSIDE_LOOP                          \
239
  /* expand each byte to 2 bytes */                       \
240
125M
  exp_dst_lo = _mm256_unpacklo_epi8(dst_reg, zero_reg);   \
241
125M
  exp_dst_hi = _mm256_unpackhi_epi8(dst_reg, zero_reg);   \
242
125M
  /* source - dest */                                     \
243
125M
  exp_src_lo = _mm256_sub_epi16(exp_src_lo, exp_dst_lo);  \
244
125M
  exp_src_hi = _mm256_sub_epi16(exp_src_hi, exp_dst_hi);  \
245
125M
  /* caculate sum */                                      \
246
125M
  *sum_reg = _mm256_add_epi16(*sum_reg, exp_src_lo);      \
247
125M
  exp_src_lo = _mm256_madd_epi16(exp_src_lo, exp_src_lo); \
248
125M
  *sum_reg = _mm256_add_epi16(*sum_reg, exp_src_hi);      \
249
125M
  exp_src_hi = _mm256_madd_epi16(exp_src_hi, exp_src_hi); \
250
125M
  /* calculate sse */                                     \
251
125M
  *sse_reg = _mm256_add_epi32(*sse_reg, exp_src_lo);      \
252
125M
  *sse_reg = _mm256_add_epi32(*sse_reg, exp_src_hi);
253
254
// final calculation to sum and sse
255
#define CALC_SUM_AND_SSE                                                   \
256
2.89M
  res_cmp = _mm256_cmpgt_epi16(zero_reg, sum_reg);                         \
257
2.89M
  sse_reg_hi = _mm256_srli_si256(sse_reg, 8);                              \
258
2.89M
  sum_reg_lo = _mm256_unpacklo_epi16(sum_reg, res_cmp);                    \
259
2.89M
  sum_reg_hi = _mm256_unpackhi_epi16(sum_reg, res_cmp);                    \
260
2.89M
  sse_reg = _mm256_add_epi32(sse_reg, sse_reg_hi);                         \
261
2.89M
  sum_reg = _mm256_add_epi32(sum_reg_lo, sum_reg_hi);                      \
262
2.89M
                                                                           \
263
2.89M
  sse_reg_hi = _mm256_srli_si256(sse_reg, 4);                              \
264
2.89M
  sum_reg_hi = _mm256_srli_si256(sum_reg, 8);                              \
265
2.89M
                                                                           \
266
2.89M
  sse_reg = _mm256_add_epi32(sse_reg, sse_reg_hi);                         \
267
2.89M
  sum_reg = _mm256_add_epi32(sum_reg, sum_reg_hi);                         \
268
2.89M
  *((int *)sse) = _mm_cvtsi128_si32(_mm256_castsi256_si128(sse_reg)) +     \
269
2.89M
                  _mm_cvtsi128_si32(_mm256_extractf128_si256(sse_reg, 1)); \
270
2.89M
  sum_reg_hi = _mm256_srli_si256(sum_reg, 4);                              \
271
2.89M
  sum_reg = _mm256_add_epi32(sum_reg, sum_reg_hi);                         \
272
2.89M
  sum = _mm_cvtsi128_si32(_mm256_castsi256_si128(sum_reg)) +               \
273
2.89M
        _mm_cvtsi128_si32(_mm256_extractf128_si256(sum_reg, 1));
274
275
static INLINE void spv32_x0_y0(const uint8_t *src, int src_stride,
276
                               const uint8_t *dst, int dst_stride,
277
                               const uint8_t *second_pred, int second_stride,
278
                               int do_sec, int height, __m256i *sum_reg,
279
96.8k
                               __m256i *sse_reg) {
280
96.8k
  const __m256i zero_reg = _mm256_setzero_si256();
281
96.8k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
282
96.8k
  int i;
283
4.34M
  for (i = 0; i < height; i++) {
284
4.25M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
285
4.25M
    const __m256i src_reg = _mm256_loadu_si256((__m256i const *)src);
286
4.25M
    if (do_sec) {
287
0
      const __m256i sec_reg = _mm256_loadu_si256((__m256i const *)second_pred);
288
0
      const __m256i avg_reg = _mm256_avg_epu8(src_reg, sec_reg);
289
0
      exp_src_lo = _mm256_unpacklo_epi8(avg_reg, zero_reg);
290
0
      exp_src_hi = _mm256_unpackhi_epi8(avg_reg, zero_reg);
291
0
      second_pred += second_stride;
292
4.25M
    } else {
293
4.25M
      exp_src_lo = _mm256_unpacklo_epi8(src_reg, zero_reg);
294
4.25M
      exp_src_hi = _mm256_unpackhi_epi8(src_reg, zero_reg);
295
4.25M
    }
296
4.25M
    CALC_SUM_SSE_INSIDE_LOOP
297
4.25M
    src += src_stride;
298
4.25M
    dst += dst_stride;
299
4.25M
  }
300
96.8k
}
301
302
// (x == 0, y == 4) or (x == 4, y == 0).  sstep determines the direction.
303
static INLINE void spv32_half_zero(const uint8_t *src, int src_stride,
304
                                   const uint8_t *dst, int dst_stride,
305
                                   const uint8_t *second_pred,
306
                                   int second_stride, int do_sec, int height,
307
                                   __m256i *sum_reg, __m256i *sse_reg,
308
948k
                                   int sstep) {
309
948k
  const __m256i zero_reg = _mm256_setzero_si256();
310
948k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
311
948k
  int i;
312
42.1M
  for (i = 0; i < height; i++) {
313
41.1M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
314
41.1M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
315
41.1M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + sstep));
316
41.1M
    const __m256i src_avg = _mm256_avg_epu8(src_0, src_1);
317
41.1M
    if (do_sec) {
318
0
      const __m256i sec_reg = _mm256_loadu_si256((__m256i const *)second_pred);
319
0
      const __m256i avg_reg = _mm256_avg_epu8(src_avg, sec_reg);
320
0
      exp_src_lo = _mm256_unpacklo_epi8(avg_reg, zero_reg);
321
0
      exp_src_hi = _mm256_unpackhi_epi8(avg_reg, zero_reg);
322
0
      second_pred += second_stride;
323
41.1M
    } else {
324
41.1M
      exp_src_lo = _mm256_unpacklo_epi8(src_avg, zero_reg);
325
41.1M
      exp_src_hi = _mm256_unpackhi_epi8(src_avg, zero_reg);
326
41.1M
    }
327
41.1M
    CALC_SUM_SSE_INSIDE_LOOP
328
41.1M
    src += src_stride;
329
41.1M
    dst += dst_stride;
330
41.1M
  }
331
948k
}
332
333
static INLINE void spv32_x0_y4(const uint8_t *src, int src_stride,
334
                               const uint8_t *dst, int dst_stride,
335
                               const uint8_t *second_pred, int second_stride,
336
                               int do_sec, int height, __m256i *sum_reg,
337
475k
                               __m256i *sse_reg) {
338
475k
  spv32_half_zero(src, src_stride, dst, dst_stride, second_pred, second_stride,
339
475k
                  do_sec, height, sum_reg, sse_reg, src_stride);
340
475k
}
341
342
static INLINE void spv32_x4_y0(const uint8_t *src, int src_stride,
343
                               const uint8_t *dst, int dst_stride,
344
                               const uint8_t *second_pred, int second_stride,
345
                               int do_sec, int height, __m256i *sum_reg,
346
472k
                               __m256i *sse_reg) {
347
472k
  spv32_half_zero(src, src_stride, dst, dst_stride, second_pred, second_stride,
348
472k
                  do_sec, height, sum_reg, sse_reg, 1);
349
472k
}
350
351
static INLINE void spv32_x4_y4(const uint8_t *src, int src_stride,
352
                               const uint8_t *dst, int dst_stride,
353
                               const uint8_t *second_pred, int second_stride,
354
                               int do_sec, int height, __m256i *sum_reg,
355
284k
                               __m256i *sse_reg) {
356
284k
  const __m256i zero_reg = _mm256_setzero_si256();
357
284k
  const __m256i src_a = _mm256_loadu_si256((__m256i const *)src);
358
284k
  const __m256i src_b = _mm256_loadu_si256((__m256i const *)(src + 1));
359
284k
  __m256i prev_src_avg = _mm256_avg_epu8(src_a, src_b);
360
284k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
361
284k
  int i;
362
284k
  src += src_stride;
363
12.4M
  for (i = 0; i < height; i++) {
364
12.1M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
365
12.1M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)(src));
366
12.1M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + 1));
367
12.1M
    const __m256i src_avg = _mm256_avg_epu8(src_0, src_1);
368
12.1M
    const __m256i current_avg = _mm256_avg_epu8(prev_src_avg, src_avg);
369
12.1M
    prev_src_avg = src_avg;
370
371
12.1M
    if (do_sec) {
372
0
      const __m256i sec_reg = _mm256_loadu_si256((__m256i const *)second_pred);
373
0
      const __m256i avg_reg = _mm256_avg_epu8(current_avg, sec_reg);
374
0
      exp_src_lo = _mm256_unpacklo_epi8(avg_reg, zero_reg);
375
0
      exp_src_hi = _mm256_unpackhi_epi8(avg_reg, zero_reg);
376
0
      second_pred += second_stride;
377
12.1M
    } else {
378
12.1M
      exp_src_lo = _mm256_unpacklo_epi8(current_avg, zero_reg);
379
12.1M
      exp_src_hi = _mm256_unpackhi_epi8(current_avg, zero_reg);
380
12.1M
    }
381
    // save current source average
382
12.1M
    CALC_SUM_SSE_INSIDE_LOOP
383
12.1M
    dst += dst_stride;
384
12.1M
    src += src_stride;
385
12.1M
  }
386
284k
}
387
388
// (x == 0, y == bil) or (x == 4, y == bil).  sstep determines the direction.
389
static INLINE void spv32_bilin_zero(const uint8_t *src, int src_stride,
390
                                    const uint8_t *dst, int dst_stride,
391
                                    const uint8_t *second_pred,
392
                                    int second_stride, int do_sec, int height,
393
                                    __m256i *sum_reg, __m256i *sse_reg,
394
841k
                                    int offset, int sstep) {
395
841k
  const __m256i zero_reg = _mm256_setzero_si256();
396
841k
  const __m256i pw8 = _mm256_set1_epi16(8);
397
841k
  const __m256i filter = _mm256_load_si256(
398
841k
      (__m256i const *)(bilinear_filters_avx2 + (offset << 5)));
399
841k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
400
841k
  int i;
401
36.8M
  for (i = 0; i < height; i++) {
402
35.9M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
403
35.9M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
404
35.9M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + sstep));
405
35.9M
    exp_src_lo = _mm256_unpacklo_epi8(src_0, src_1);
406
35.9M
    exp_src_hi = _mm256_unpackhi_epi8(src_0, src_1);
407
408
35.9M
    FILTER_SRC(filter)
409
35.9M
    if (do_sec) {
410
0
      const __m256i sec_reg = _mm256_loadu_si256((__m256i const *)second_pred);
411
0
      const __m256i exp_src = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
412
0
      const __m256i avg_reg = _mm256_avg_epu8(exp_src, sec_reg);
413
0
      second_pred += second_stride;
414
0
      exp_src_lo = _mm256_unpacklo_epi8(avg_reg, zero_reg);
415
0
      exp_src_hi = _mm256_unpackhi_epi8(avg_reg, zero_reg);
416
0
    }
417
35.9M
    CALC_SUM_SSE_INSIDE_LOOP
418
35.9M
    src += src_stride;
419
35.9M
    dst += dst_stride;
420
35.9M
  }
421
841k
}
422
423
static INLINE void spv32_x0_yb(const uint8_t *src, int src_stride,
424
                               const uint8_t *dst, int dst_stride,
425
                               const uint8_t *second_pred, int second_stride,
426
                               int do_sec, int height, __m256i *sum_reg,
427
435k
                               __m256i *sse_reg, int y_offset) {
428
435k
  spv32_bilin_zero(src, src_stride, dst, dst_stride, second_pred, second_stride,
429
435k
                   do_sec, height, sum_reg, sse_reg, y_offset, src_stride);
430
435k
}
431
432
static INLINE void spv32_xb_y0(const uint8_t *src, int src_stride,
433
                               const uint8_t *dst, int dst_stride,
434
                               const uint8_t *second_pred, int second_stride,
435
                               int do_sec, int height, __m256i *sum_reg,
436
406k
                               __m256i *sse_reg, int x_offset) {
437
406k
  spv32_bilin_zero(src, src_stride, dst, dst_stride, second_pred, second_stride,
438
406k
                   do_sec, height, sum_reg, sse_reg, x_offset, 1);
439
406k
}
440
441
static INLINE void spv32_x4_yb(const uint8_t *src, int src_stride,
442
                               const uint8_t *dst, int dst_stride,
443
                               const uint8_t *second_pred, int second_stride,
444
                               int do_sec, int height, __m256i *sum_reg,
445
145k
                               __m256i *sse_reg, int y_offset) {
446
145k
  const __m256i zero_reg = _mm256_setzero_si256();
447
145k
  const __m256i pw8 = _mm256_set1_epi16(8);
448
145k
  const __m256i filter = _mm256_load_si256(
449
145k
      (__m256i const *)(bilinear_filters_avx2 + (y_offset << 5)));
450
145k
  const __m256i src_a = _mm256_loadu_si256((__m256i const *)src);
451
145k
  const __m256i src_b = _mm256_loadu_si256((__m256i const *)(src + 1));
452
145k
  __m256i prev_src_avg = _mm256_avg_epu8(src_a, src_b);
453
145k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
454
145k
  int i;
455
145k
  src += src_stride;
456
6.58M
  for (i = 0; i < height; i++) {
457
6.43M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
458
6.43M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
459
6.43M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + 1));
460
6.43M
    const __m256i src_avg = _mm256_avg_epu8(src_0, src_1);
461
6.43M
    exp_src_lo = _mm256_unpacklo_epi8(prev_src_avg, src_avg);
462
6.43M
    exp_src_hi = _mm256_unpackhi_epi8(prev_src_avg, src_avg);
463
6.43M
    prev_src_avg = src_avg;
464
465
6.43M
    FILTER_SRC(filter)
466
6.43M
    if (do_sec) {
467
0
      const __m256i sec_reg = _mm256_loadu_si256((__m256i const *)second_pred);
468
0
      const __m256i exp_src_avg = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
469
0
      const __m256i avg_reg = _mm256_avg_epu8(exp_src_avg, sec_reg);
470
0
      exp_src_lo = _mm256_unpacklo_epi8(avg_reg, zero_reg);
471
0
      exp_src_hi = _mm256_unpackhi_epi8(avg_reg, zero_reg);
472
0
      second_pred += second_stride;
473
0
    }
474
6.43M
    CALC_SUM_SSE_INSIDE_LOOP
475
6.43M
    dst += dst_stride;
476
6.43M
    src += src_stride;
477
6.43M
  }
478
145k
}
479
480
static INLINE void spv32_xb_y4(const uint8_t *src, int src_stride,
481
                               const uint8_t *dst, int dst_stride,
482
                               const uint8_t *second_pred, int second_stride,
483
                               int do_sec, int height, __m256i *sum_reg,
484
164k
                               __m256i *sse_reg, int x_offset) {
485
164k
  const __m256i zero_reg = _mm256_setzero_si256();
486
164k
  const __m256i pw8 = _mm256_set1_epi16(8);
487
164k
  const __m256i filter = _mm256_load_si256(
488
164k
      (__m256i const *)(bilinear_filters_avx2 + (x_offset << 5)));
489
164k
  const __m256i src_a = _mm256_loadu_si256((__m256i const *)src);
490
164k
  const __m256i src_b = _mm256_loadu_si256((__m256i const *)(src + 1));
491
164k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
492
164k
  __m256i src_reg, src_pack;
493
164k
  int i;
494
164k
  exp_src_lo = _mm256_unpacklo_epi8(src_a, src_b);
495
164k
  exp_src_hi = _mm256_unpackhi_epi8(src_a, src_b);
496
164k
  FILTER_SRC(filter)
497
  // convert each 16 bit to 8 bit to each low and high lane source
498
164k
  src_pack = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
499
500
164k
  src += src_stride;
501
7.36M
  for (i = 0; i < height; i++) {
502
7.20M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
503
7.20M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
504
7.20M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + 1));
505
7.20M
    exp_src_lo = _mm256_unpacklo_epi8(src_0, src_1);
506
7.20M
    exp_src_hi = _mm256_unpackhi_epi8(src_0, src_1);
507
508
7.20M
    FILTER_SRC(filter)
509
510
7.20M
    src_reg = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
511
    // average between previous pack to the current
512
7.20M
    src_pack = _mm256_avg_epu8(src_pack, src_reg);
513
514
7.20M
    if (do_sec) {
515
0
      const __m256i sec_reg = _mm256_loadu_si256((__m256i const *)second_pred);
516
0
      const __m256i avg_pack = _mm256_avg_epu8(src_pack, sec_reg);
517
0
      exp_src_lo = _mm256_unpacklo_epi8(avg_pack, zero_reg);
518
0
      exp_src_hi = _mm256_unpackhi_epi8(avg_pack, zero_reg);
519
0
      second_pred += second_stride;
520
7.20M
    } else {
521
7.20M
      exp_src_lo = _mm256_unpacklo_epi8(src_pack, zero_reg);
522
7.20M
      exp_src_hi = _mm256_unpackhi_epi8(src_pack, zero_reg);
523
7.20M
    }
524
7.20M
    CALC_SUM_SSE_INSIDE_LOOP
525
7.20M
    src_pack = src_reg;
526
7.20M
    dst += dst_stride;
527
7.20M
    src += src_stride;
528
7.20M
  }
529
164k
}
530
531
static INLINE void spv32_xb_yb(const uint8_t *src, int src_stride,
532
                               const uint8_t *dst, int dst_stride,
533
                               const uint8_t *second_pred, int second_stride,
534
                               int do_sec, int height, __m256i *sum_reg,
535
415k
                               __m256i *sse_reg, int x_offset, int y_offset) {
536
415k
  const __m256i zero_reg = _mm256_setzero_si256();
537
415k
  const __m256i pw8 = _mm256_set1_epi16(8);
538
415k
  const __m256i xfilter = _mm256_load_si256(
539
415k
      (__m256i const *)(bilinear_filters_avx2 + (x_offset << 5)));
540
415k
  const __m256i yfilter = _mm256_load_si256(
541
415k
      (__m256i const *)(bilinear_filters_avx2 + (y_offset << 5)));
542
415k
  const __m256i src_a = _mm256_loadu_si256((__m256i const *)src);
543
415k
  const __m256i src_b = _mm256_loadu_si256((__m256i const *)(src + 1));
544
415k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
545
415k
  __m256i prev_src_pack, src_pack;
546
415k
  int i;
547
415k
  exp_src_lo = _mm256_unpacklo_epi8(src_a, src_b);
548
415k
  exp_src_hi = _mm256_unpackhi_epi8(src_a, src_b);
549
415k
  FILTER_SRC(xfilter)
550
  // convert each 16 bit to 8 bit to each low and high lane source
551
415k
  prev_src_pack = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
552
415k
  src += src_stride;
553
554
18.2M
  for (i = 0; i < height; i++) {
555
17.8M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
556
17.8M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
557
17.8M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + 1));
558
17.8M
    exp_src_lo = _mm256_unpacklo_epi8(src_0, src_1);
559
17.8M
    exp_src_hi = _mm256_unpackhi_epi8(src_0, src_1);
560
561
17.8M
    FILTER_SRC(xfilter)
562
17.8M
    src_pack = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
563
564
    // merge previous pack to current pack source
565
17.8M
    exp_src_lo = _mm256_unpacklo_epi8(prev_src_pack, src_pack);
566
17.8M
    exp_src_hi = _mm256_unpackhi_epi8(prev_src_pack, src_pack);
567
568
17.8M
    FILTER_SRC(yfilter)
569
17.8M
    if (do_sec) {
570
0
      const __m256i sec_reg = _mm256_loadu_si256((__m256i const *)second_pred);
571
0
      const __m256i exp_src = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
572
0
      const __m256i avg_reg = _mm256_avg_epu8(exp_src, sec_reg);
573
0
      exp_src_lo = _mm256_unpacklo_epi8(avg_reg, zero_reg);
574
0
      exp_src_hi = _mm256_unpackhi_epi8(avg_reg, zero_reg);
575
0
      second_pred += second_stride;
576
0
    }
577
578
17.8M
    prev_src_pack = src_pack;
579
580
17.8M
    CALC_SUM_SSE_INSIDE_LOOP
581
17.8M
    dst += dst_stride;
582
17.8M
    src += src_stride;
583
17.8M
  }
584
415k
}
585
586
static INLINE int sub_pix_var32xh(const uint8_t *src, int src_stride,
587
                                  int x_offset, int y_offset,
588
                                  const uint8_t *dst, int dst_stride,
589
                                  const uint8_t *second_pred, int second_stride,
590
2.89M
                                  int do_sec, int height, unsigned int *sse) {
591
2.89M
  const __m256i zero_reg = _mm256_setzero_si256();
592
2.89M
  __m256i sum_reg = _mm256_setzero_si256();
593
2.89M
  __m256i sse_reg = _mm256_setzero_si256();
594
2.89M
  __m256i sse_reg_hi, res_cmp, sum_reg_lo, sum_reg_hi;
595
2.89M
  int sum;
596
  // x_offset = 0 and y_offset = 0
597
2.89M
  if (x_offset == 0) {
598
1.00M
    if (y_offset == 0) {
599
96.8k
      spv32_x0_y0(src, src_stride, dst, dst_stride, second_pred, second_stride,
600
96.8k
                  do_sec, height, &sum_reg, &sse_reg);
601
      // x_offset = 0 and y_offset = 4
602
911k
    } else if (y_offset == 4) {
603
475k
      spv32_x0_y4(src, src_stride, dst, dst_stride, second_pred, second_stride,
604
475k
                  do_sec, height, &sum_reg, &sse_reg);
605
      // x_offset = 0 and y_offset = bilin interpolation
606
475k
    } else {
607
435k
      spv32_x0_yb(src, src_stride, dst, dst_stride, second_pred, second_stride,
608
435k
                  do_sec, height, &sum_reg, &sse_reg, y_offset);
609
435k
    }
610
    // x_offset = 4  and y_offset = 0
611
1.88M
  } else if (x_offset == 4) {
612
902k
    if (y_offset == 0) {
613
472k
      spv32_x4_y0(src, src_stride, dst, dst_stride, second_pred, second_stride,
614
472k
                  do_sec, height, &sum_reg, &sse_reg);
615
      // x_offset = 4  and y_offset = 4
616
472k
    } else if (y_offset == 4) {
617
284k
      spv32_x4_y4(src, src_stride, dst, dst_stride, second_pred, second_stride,
618
284k
                  do_sec, height, &sum_reg, &sse_reg);
619
      // x_offset = 4  and y_offset = bilin interpolation
620
284k
    } else {
621
145k
      spv32_x4_yb(src, src_stride, dst, dst_stride, second_pred, second_stride,
622
145k
                  do_sec, height, &sum_reg, &sse_reg, y_offset);
623
145k
    }
624
    // x_offset = bilin interpolation and y_offset = 0
625
986k
  } else {
626
986k
    if (y_offset == 0) {
627
406k
      spv32_xb_y0(src, src_stride, dst, dst_stride, second_pred, second_stride,
628
406k
                  do_sec, height, &sum_reg, &sse_reg, x_offset);
629
      // x_offset = bilin interpolation and y_offset = 4
630
580k
    } else if (y_offset == 4) {
631
164k
      spv32_xb_y4(src, src_stride, dst, dst_stride, second_pred, second_stride,
632
164k
                  do_sec, height, &sum_reg, &sse_reg, x_offset);
633
      // x_offset = bilin interpolation and y_offset = bilin interpolation
634
415k
    } else {
635
415k
      spv32_xb_yb(src, src_stride, dst, dst_stride, second_pred, second_stride,
636
415k
                  do_sec, height, &sum_reg, &sse_reg, x_offset, y_offset);
637
415k
    }
638
986k
  }
639
2.89M
  CALC_SUM_AND_SSE
640
2.89M
  return sum;
641
2.89M
}
642
643
static int sub_pixel_variance32xh_avx2(const uint8_t *src, int src_stride,
644
                                       int x_offset, int y_offset,
645
                                       const uint8_t *dst, int dst_stride,
646
2.89M
                                       int height, unsigned int *sse) {
647
2.89M
  return sub_pix_var32xh(src, src_stride, x_offset, y_offset, dst, dst_stride,
648
2.89M
                         NULL, 0, 0, height, sse);
649
2.89M
}
650
651
static int sub_pixel_avg_variance32xh_avx2(const uint8_t *src, int src_stride,
652
                                           int x_offset, int y_offset,
653
                                           const uint8_t *dst, int dst_stride,
654
                                           const uint8_t *second_pred,
655
                                           int second_stride, int height,
656
0
                                           unsigned int *sse) {
657
0
  return sub_pix_var32xh(src, src_stride, x_offset, y_offset, dst, dst_stride,
658
0
                         second_pred, second_stride, 1, height, sse);
659
0
}
660
661
typedef void (*get_var_avx2)(const uint8_t *src_ptr, int src_stride,
662
                             const uint8_t *ref_ptr, int ref_stride,
663
                             unsigned int *sse, int *sum);
664
665
unsigned int vpx_variance8x4_avx2(const uint8_t *src_ptr, int src_stride,
666
                                  const uint8_t *ref_ptr, int ref_stride,
667
10.8M
                                  unsigned int *sse) {
668
10.8M
  __m256i vsse, vsum;
669
10.8M
  int sum;
670
10.8M
  variance8_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 4, &vsse, &vsum);
671
10.8M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
672
10.8M
  return *sse - ((sum * sum) >> 5);
673
10.8M
}
674
675
unsigned int vpx_variance8x8_avx2(const uint8_t *src_ptr, int src_stride,
676
                                  const uint8_t *ref_ptr, int ref_stride,
677
148M
                                  unsigned int *sse) {
678
148M
  __m256i vsse, vsum;
679
148M
  int sum;
680
148M
  variance8_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 8, &vsse, &vsum);
681
148M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
682
148M
  return *sse - ((sum * sum) >> 6);
683
148M
}
684
685
unsigned int vpx_variance8x16_avx2(const uint8_t *src_ptr, int src_stride,
686
                                   const uint8_t *ref_ptr, int ref_stride,
687
8.34M
                                   unsigned int *sse) {
688
8.34M
  __m256i vsse, vsum;
689
8.34M
  int sum;
690
8.34M
  variance8_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
691
8.34M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
692
8.34M
  return *sse - ((sum * sum) >> 7);
693
8.34M
}
694
695
unsigned int vpx_variance16x8_avx2(const uint8_t *src_ptr, int src_stride,
696
                                   const uint8_t *ref_ptr, int ref_stride,
697
8.26M
                                   unsigned int *sse) {
698
8.26M
  int sum;
699
8.26M
  __m256i vsse, vsum;
700
8.26M
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 8, &vsse, &vsum);
701
8.26M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
702
8.26M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 7);
703
8.26M
}
704
705
unsigned int vpx_variance16x16_avx2(const uint8_t *src_ptr, int src_stride,
706
                                    const uint8_t *ref_ptr, int ref_stride,
707
43.8M
                                    unsigned int *sse) {
708
43.8M
  int sum;
709
43.8M
  __m256i vsse, vsum;
710
43.8M
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
711
43.8M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
712
43.8M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 8);
713
43.8M
}
714
715
unsigned int vpx_variance16x32_avx2(const uint8_t *src_ptr, int src_stride,
716
                                    const uint8_t *ref_ptr, int ref_stride,
717
1.82M
                                    unsigned int *sse) {
718
1.82M
  int sum;
719
1.82M
  __m256i vsse, vsum;
720
1.82M
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 32, &vsse, &vsum);
721
1.82M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
722
1.82M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 9);
723
1.82M
}
724
725
unsigned int vpx_variance32x16_avx2(const uint8_t *src_ptr, int src_stride,
726
                                    const uint8_t *ref_ptr, int ref_stride,
727
2.09M
                                    unsigned int *sse) {
728
2.09M
  int sum;
729
2.09M
  __m256i vsse, vsum;
730
2.09M
  variance32_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
731
2.09M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
732
2.09M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 9);
733
2.09M
}
734
735
unsigned int vpx_variance32x32_avx2(const uint8_t *src_ptr, int src_stride,
736
                                    const uint8_t *ref_ptr, int ref_stride,
737
7.80M
                                    unsigned int *sse) {
738
7.80M
  int sum;
739
7.80M
  __m256i vsse, vsum;
740
7.80M
  __m128i vsum_128;
741
7.80M
  variance32_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 32, &vsse, &vsum);
742
7.80M
  vsum_128 = _mm_add_epi16(_mm256_castsi256_si128(vsum),
743
7.80M
                           _mm256_extractf128_si256(vsum, 1));
744
7.80M
  vsum_128 = _mm_add_epi32(_mm_cvtepi16_epi32(vsum_128),
745
7.80M
                           _mm_cvtepi16_epi32(_mm_srli_si128(vsum_128, 8)));
746
7.80M
  variance_final_from_32bit_sum_avx2(vsse, vsum_128, sse, &sum);
747
7.80M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 10);
748
7.80M
}
749
750
unsigned int vpx_variance32x64_avx2(const uint8_t *src_ptr, int src_stride,
751
                                    const uint8_t *ref_ptr, int ref_stride,
752
373k
                                    unsigned int *sse) {
753
373k
  int sum;
754
373k
  __m256i vsse, vsum;
755
373k
  __m128i vsum_128;
756
373k
  variance32_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 64, &vsse, &vsum);
757
373k
  vsum = sum_to_32bit_avx2(vsum);
758
373k
  vsum_128 = _mm_add_epi32(_mm256_castsi256_si128(vsum),
759
373k
                           _mm256_extractf128_si256(vsum, 1));
760
373k
  variance_final_from_32bit_sum_avx2(vsse, vsum_128, sse, &sum);
761
373k
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 11);
762
373k
}
763
764
unsigned int vpx_variance64x32_avx2(const uint8_t *src_ptr, int src_stride,
765
                                    const uint8_t *ref_ptr, int ref_stride,
766
620k
                                    unsigned int *sse) {
767
620k
  __m256i vsse = _mm256_setzero_si256();
768
620k
  __m256i vsum = _mm256_setzero_si256();
769
620k
  __m128i vsum_128;
770
620k
  int sum;
771
620k
  variance64_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 32, &vsse, &vsum);
772
620k
  vsum = sum_to_32bit_avx2(vsum);
773
620k
  vsum_128 = _mm_add_epi32(_mm256_castsi256_si128(vsum),
774
620k
                           _mm256_extractf128_si256(vsum, 1));
775
620k
  variance_final_from_32bit_sum_avx2(vsse, vsum_128, sse, &sum);
776
620k
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 11);
777
620k
}
778
779
unsigned int vpx_variance64x64_avx2(const uint8_t *src_ptr, int src_stride,
780
                                    const uint8_t *ref_ptr, int ref_stride,
781
644k
                                    unsigned int *sse) {
782
644k
  __m256i vsse = _mm256_setzero_si256();
783
644k
  __m256i vsum = _mm256_setzero_si256();
784
644k
  __m128i vsum_128;
785
644k
  int sum;
786
644k
  int i = 0;
787
788
1.93M
  for (i = 0; i < 2; i++) {
789
1.28M
    __m256i vsum16;
790
1.28M
    variance64_avx2(src_ptr + 32 * i * src_stride, src_stride,
791
1.28M
                    ref_ptr + 32 * i * ref_stride, ref_stride, 32, &vsse,
792
1.28M
                    &vsum16);
793
1.28M
    vsum = _mm256_add_epi32(vsum, sum_to_32bit_avx2(vsum16));
794
1.28M
  }
795
644k
  vsum_128 = _mm_add_epi32(_mm256_castsi256_si128(vsum),
796
644k
                           _mm256_extractf128_si256(vsum, 1));
797
644k
  variance_final_from_32bit_sum_avx2(vsse, vsum_128, sse, &sum);
798
644k
  return *sse - (unsigned int)(((int64_t)sum * sum) >> 12);
799
644k
}
800
801
unsigned int vpx_mse16x8_avx2(const uint8_t *src_ptr, int src_stride,
802
                              const uint8_t *ref_ptr, int ref_stride,
803
0
                              unsigned int *sse) {
804
0
  int sum;
805
0
  __m256i vsse, vsum;
806
0
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 8, &vsse, &vsum);
807
0
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
808
0
  return *sse;
809
0
}
810
811
unsigned int vpx_mse16x16_avx2(const uint8_t *src_ptr, int src_stride,
812
                               const uint8_t *ref_ptr, int ref_stride,
813
12.6M
                               unsigned int *sse) {
814
12.6M
  int sum;
815
12.6M
  __m256i vsse, vsum;
816
12.6M
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
817
12.6M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
818
12.6M
  return *sse;
819
12.6M
}
820
821
unsigned int vpx_sub_pixel_variance64x64_avx2(
822
    const uint8_t *src_ptr, int src_stride, int x_offset, int y_offset,
823
504k
    const uint8_t *ref_ptr, int ref_stride, unsigned int *sse) {
824
504k
  unsigned int sse1;
825
504k
  const int se1 = sub_pixel_variance32xh_avx2(
826
504k
      src_ptr, src_stride, x_offset, y_offset, ref_ptr, ref_stride, 64, &sse1);
827
504k
  unsigned int sse2;
828
504k
  const int se2 =
829
504k
      sub_pixel_variance32xh_avx2(src_ptr + 32, src_stride, x_offset, y_offset,
830
504k
                                  ref_ptr + 32, ref_stride, 64, &sse2);
831
504k
  const int se = se1 + se2;
832
504k
  *sse = sse1 + sse2;
833
504k
  return *sse - (uint32_t)(((int64_t)se * se) >> 12);
834
504k
}
835
836
unsigned int vpx_sub_pixel_variance32x32_avx2(
837
    const uint8_t *src_ptr, int src_stride, int x_offset, int y_offset,
838
1.88M
    const uint8_t *ref_ptr, int ref_stride, unsigned int *sse) {
839
1.88M
  const int se = sub_pixel_variance32xh_avx2(
840
1.88M
      src_ptr, src_stride, x_offset, y_offset, ref_ptr, ref_stride, 32, sse);
841
1.88M
  return *sse - (uint32_t)(((int64_t)se * se) >> 10);
842
1.88M
}
843
844
unsigned int vpx_sub_pixel_avg_variance64x64_avx2(
845
    const uint8_t *src_ptr, int src_stride, int x_offset, int y_offset,
846
    const uint8_t *ref_ptr, int ref_stride, unsigned int *sse,
847
0
    const uint8_t *second_pred) {
848
0
  unsigned int sse1;
849
0
  const int se1 = sub_pixel_avg_variance32xh_avx2(src_ptr, src_stride, x_offset,
850
0
                                                  y_offset, ref_ptr, ref_stride,
851
0
                                                  second_pred, 64, 64, &sse1);
852
0
  unsigned int sse2;
853
0
  const int se2 = sub_pixel_avg_variance32xh_avx2(
854
0
      src_ptr + 32, src_stride, x_offset, y_offset, ref_ptr + 32, ref_stride,
855
0
      second_pred + 32, 64, 64, &sse2);
856
0
  const int se = se1 + se2;
857
858
0
  *sse = sse1 + sse2;
859
860
0
  return *sse - (uint32_t)(((int64_t)se * se) >> 12);
861
0
}
862
863
unsigned int vpx_sub_pixel_avg_variance32x32_avx2(
864
    const uint8_t *src_ptr, int src_stride, int x_offset, int y_offset,
865
    const uint8_t *ref_ptr, int ref_stride, unsigned int *sse,
866
0
    const uint8_t *second_pred) {
867
  // Process 32 elements in parallel.
868
0
  const int se = sub_pixel_avg_variance32xh_avx2(src_ptr, src_stride, x_offset,
869
0
                                                 y_offset, ref_ptr, ref_stride,
870
0
                                                 second_pred, 32, 32, sse);
871
0
  return *sse - (uint32_t)(((int64_t)se * se) >> 10);
872
0
}