Coverage Report

Created: 2025-08-28 07:12

/src/libvpx/vpx_dsp/x86/variance_avx2.c
Line
Count
Source (jump to first uncovered line)
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
931M
                                        __m256i *const sum) {
44
931M
  const __m256i adj_sub = _mm256_load_si256((__m256i const *)adjacent_sub_avx2);
45
46
  // unpack into pairs of source and reference values
47
931M
  const __m256i src_ref0 = _mm256_unpacklo_epi8(src, ref);
48
931M
  const __m256i src_ref1 = _mm256_unpackhi_epi8(src, ref);
49
50
  // subtract adjacent elements using src*1 + ref*-1
51
931M
  const __m256i diff0 = _mm256_maddubs_epi16(src_ref0, adj_sub);
52
931M
  const __m256i diff1 = _mm256_maddubs_epi16(src_ref1, adj_sub);
53
931M
  const __m256i madd0 = _mm256_madd_epi16(diff0, diff0);
54
931M
  const __m256i madd1 = _mm256_madd_epi16(diff1, diff1);
55
56
  // add to the running totals
57
931M
  *sum = _mm256_add_epi16(*sum, _mm256_add_epi16(diff0, diff1));
58
931M
  *sse = _mm256_add_epi32(*sse, _mm256_add_epi32(madd0, madd1));
59
931M
}
60
61
static INLINE void variance_final_from_32bit_sum_avx2(__m256i vsse,
62
                                                      __m128i vsum,
63
                                                      unsigned int *const sse,
64
241M
                                                      int *const sum) {
65
  // extract the low lane and add it to the high lane
66
241M
  const __m128i sse_reg_128 = _mm_add_epi32(_mm256_castsi256_si128(vsse),
67
241M
                                            _mm256_extractf128_si256(vsse, 1));
68
69
  // unpack sse and sum registers and add
70
241M
  const __m128i sse_sum_lo = _mm_unpacklo_epi32(sse_reg_128, vsum);
71
241M
  const __m128i sse_sum_hi = _mm_unpackhi_epi32(sse_reg_128, vsum);
72
241M
  const __m128i sse_sum = _mm_add_epi32(sse_sum_lo, sse_sum_hi);
73
74
  // perform the final summation and extract the results
75
241M
  const __m128i res = _mm_add_epi32(sse_sum, _mm_srli_si128(sse_sum, 8));
76
241M
  *((int *)sse) = _mm_cvtsi128_si32(res);
77
241M
  *((int *)sum) = _mm_extract_epi32(res, 1);
78
241M
}
79
80
static INLINE void variance_final_from_16bit_sum_avx2(__m256i vsse,
81
                                                      __m256i vsum,
82
                                                      unsigned int *const sse,
83
232M
                                                      int *const sum) {
84
  // extract the low lane and add it to the high lane
85
232M
  const __m128i sum_reg_128 = _mm_add_epi16(_mm256_castsi256_si128(vsum),
86
232M
                                            _mm256_extractf128_si256(vsum, 1));
87
232M
  const __m128i sum_reg_64 =
88
232M
      _mm_add_epi16(sum_reg_128, _mm_srli_si128(sum_reg_128, 8));
89
232M
  const __m128i sum_int32 = _mm_cvtepi16_epi32(sum_reg_64);
90
91
232M
  variance_final_from_32bit_sum_avx2(vsse, sum_int32, sse, sum);
92
232M
}
93
94
2.27M
static INLINE __m256i sum_to_32bit_avx2(const __m256i sum) {
95
2.27M
  const __m256i sum_lo = _mm256_cvtepi16_epi32(_mm256_castsi256_si128(sum));
96
2.27M
  const __m256i sum_hi =
97
2.27M
      _mm256_cvtepi16_epi32(_mm256_extractf128_si256(sum, 1));
98
2.27M
  return _mm256_add_epi32(sum_lo, sum_hi);
99
2.27M
}
100
101
static INLINE void variance8_kernel_avx2(
102
    const uint8_t *const src, const int src_stride, const uint8_t *const ref,
103
670M
    const int ref_stride, __m256i *const sse, __m256i *const sum) {
104
670M
  __m128i src0, src1, ref0, ref1;
105
670M
  __m256i ss, rr, diff;
106
107
  // 0 0 0.... 0 s07 s06 s05 s04 s03 s02 s01 s00
108
670M
  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
670M
  src1 = _mm_loadl_epi64((const __m128i *)(src + 1 * src_stride));
112
113
  // s17 s16...s11 s10 s07 s06...s01 s00 (8bit)
114
670M
  src0 = _mm_unpacklo_epi64(src0, src1);
115
116
  // s17 s16...s11 s10 s07 s06...s01 s00 (16 bit)
117
670M
  ss = _mm256_cvtepu8_epi16(src0);
118
119
  // 0 0 0.... 0 r07 r06 r05 r04 r03 r02 r01 r00
120
670M
  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
670M
  ref1 = _mm_loadl_epi64((const __m128i *)(ref + 1 * ref_stride));
124
125
  // r17 r16...r11 r10 r07 r06...r01 r00 (8 bit)
126
670M
  ref0 = _mm_unpacklo_epi64(ref0, ref1);
127
128
  // r17 r16...r11 r10 r07 r06...r01 r00 (16 bit)
129
670M
  rr = _mm256_cvtepu8_epi16(ref0);
130
131
670M
  diff = _mm256_sub_epi16(ss, rr);
132
670M
  *sse = _mm256_add_epi32(*sse, _mm256_madd_epi16(diff, diff));
133
670M
  *sum = _mm256_add_epi16(*sum, diff);
134
670M
}
135
136
static INLINE void variance16_kernel_avx2(
137
    const uint8_t *const src, const int src_stride, const uint8_t *const ref,
138
503M
    const int ref_stride, __m256i *const sse, __m256i *const sum) {
139
503M
  const __m128i s0 = _mm_loadu_si128((__m128i const *)(src + 0 * src_stride));
140
503M
  const __m128i s1 = _mm_loadu_si128((__m128i const *)(src + 1 * src_stride));
141
503M
  const __m128i r0 = _mm_loadu_si128((__m128i const *)(ref + 0 * ref_stride));
142
503M
  const __m128i r1 = _mm_loadu_si128((__m128i const *)(ref + 1 * ref_stride));
143
503M
  const __m256i s = _mm256_inserti128_si256(_mm256_castsi128_si256(s0), s1, 1);
144
503M
  const __m256i r = _mm256_inserti128_si256(_mm256_castsi128_si256(r0), r1, 1);
145
503M
  variance_kernel_avx2(s, r, sse, sum);
146
503M
}
147
148
static INLINE void variance32_kernel_avx2(const uint8_t *const src,
149
                                          const uint8_t *const ref,
150
                                          __m256i *const sse,
151
427M
                                          __m256i *const sum) {
152
427M
  const __m256i s = _mm256_loadu_si256((__m256i const *)(src));
153
427M
  const __m256i r = _mm256_loadu_si256((__m256i const *)(ref));
154
427M
  variance_kernel_avx2(s, r, sse, sum);
155
427M
}
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
164M
                                  __m256i *const vsum) {
161
164M
  int i;
162
164M
  *vsum = _mm256_setzero_si256();
163
164M
  *vsse = _mm256_setzero_si256();
164
165
835M
  for (i = 0; i < h; i += 2) {
166
670M
    variance8_kernel_avx2(src, src_stride, ref, ref_stride, vsse, vsum);
167
670M
    src += 2 * src_stride;
168
670M
    ref += 2 * ref_stride;
169
670M
  }
170
164M
}
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
65.1M
                                   __m256i *const vsum) {
176
65.1M
  int i;
177
65.1M
  *vsum = _mm256_setzero_si256();
178
65.1M
  *vsse = _mm256_setzero_si256();
179
180
568M
  for (i = 0; i < h; i += 2) {
181
503M
    variance16_kernel_avx2(src, src_stride, ref, ref_stride, vsse, vsum);
182
503M
    src += 2 * src_stride;
183
503M
    ref += 2 * ref_stride;
184
503M
  }
185
65.1M
}
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
316M
  for (i = 0; i < h; i++) {
196
305M
    variance32_kernel_avx2(src, ref, vsse, vsum);
197
305M
    src += src_stride;
198
305M
    ref += ref_stride;
199
305M
  }
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
62.7M
  for (i = 0; i < h; i++) {
210
60.8M
    variance32_kernel_avx2(src + 0, ref + 0, vsse, vsum);
211
60.8M
    variance32_kernel_avx2(src + 32, ref + 32, vsse, vsum);
212
60.8M
    src += src_stride;
213
60.8M
    ref += ref_stride;
214
60.8M
  }
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
84.5M
  exp_src_lo = _mm256_maddubs_epi16(exp_src_lo, filter); \
228
84.5M
  exp_src_hi = _mm256_maddubs_epi16(exp_src_hi, filter); \
229
84.5M
                                                         \
230
84.5M
  /* add 8 to source */                                  \
231
84.5M
  exp_src_lo = _mm256_add_epi16(exp_src_lo, pw8);        \
232
84.5M
  exp_src_hi = _mm256_add_epi16(exp_src_hi, pw8);        \
233
84.5M
                                                         \
234
84.5M
  /* divide source by 16 */                              \
235
84.5M
  exp_src_lo = _mm256_srai_epi16(exp_src_lo, 4);         \
236
84.5M
  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
123M
  exp_dst_lo = _mm256_unpacklo_epi8(dst_reg, zero_reg);   \
241
123M
  exp_dst_hi = _mm256_unpackhi_epi8(dst_reg, zero_reg);   \
242
123M
  /* source - dest */                                     \
243
123M
  exp_src_lo = _mm256_sub_epi16(exp_src_lo, exp_dst_lo);  \
244
123M
  exp_src_hi = _mm256_sub_epi16(exp_src_hi, exp_dst_hi);  \
245
123M
  /* caculate sum */                                      \
246
123M
  *sum_reg = _mm256_add_epi16(*sum_reg, exp_src_lo);      \
247
123M
  exp_src_lo = _mm256_madd_epi16(exp_src_lo, exp_src_lo); \
248
123M
  *sum_reg = _mm256_add_epi16(*sum_reg, exp_src_hi);      \
249
123M
  exp_src_hi = _mm256_madd_epi16(exp_src_hi, exp_src_hi); \
250
123M
  /* calculate sse */                                     \
251
123M
  *sse_reg = _mm256_add_epi32(*sse_reg, exp_src_lo);      \
252
123M
  *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.86M
  res_cmp = _mm256_cmpgt_epi16(zero_reg, sum_reg);                         \
257
2.86M
  sse_reg_hi = _mm256_srli_si256(sse_reg, 8);                              \
258
2.86M
  sum_reg_lo = _mm256_unpacklo_epi16(sum_reg, res_cmp);                    \
259
2.86M
  sum_reg_hi = _mm256_unpackhi_epi16(sum_reg, res_cmp);                    \
260
2.86M
  sse_reg = _mm256_add_epi32(sse_reg, sse_reg_hi);                         \
261
2.86M
  sum_reg = _mm256_add_epi32(sum_reg_lo, sum_reg_hi);                      \
262
2.86M
                                                                           \
263
2.86M
  sse_reg_hi = _mm256_srli_si256(sse_reg, 4);                              \
264
2.86M
  sum_reg_hi = _mm256_srli_si256(sum_reg, 8);                              \
265
2.86M
                                                                           \
266
2.86M
  sse_reg = _mm256_add_epi32(sse_reg, sse_reg_hi);                         \
267
2.86M
  sum_reg = _mm256_add_epi32(sum_reg, sum_reg_hi);                         \
268
2.86M
  *((int *)sse) = _mm_cvtsi128_si32(_mm256_castsi256_si128(sse_reg)) +     \
269
2.86M
                  _mm_cvtsi128_si32(_mm256_extractf128_si256(sse_reg, 1)); \
270
2.86M
  sum_reg_hi = _mm256_srli_si256(sum_reg, 4);                              \
271
2.86M
  sum_reg = _mm256_add_epi32(sum_reg, sum_reg_hi);                         \
272
2.86M
  sum = _mm_cvtsi128_si32(_mm256_castsi256_si128(sum_reg)) +               \
273
2.86M
        _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.0k
                               __m256i *sse_reg) {
280
96.0k
  const __m256i zero_reg = _mm256_setzero_si256();
281
96.0k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
282
96.0k
  int i;
283
4.30M
  for (i = 0; i < height; i++) {
284
4.20M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
285
4.20M
    const __m256i src_reg = _mm256_loadu_si256((__m256i const *)src);
286
4.20M
    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.20M
    } else {
293
4.20M
      exp_src_lo = _mm256_unpacklo_epi8(src_reg, zero_reg);
294
4.20M
      exp_src_hi = _mm256_unpackhi_epi8(src_reg, zero_reg);
295
4.20M
    }
296
4.20M
    CALC_SUM_SSE_INSIDE_LOOP
297
4.20M
    src += src_stride;
298
4.20M
    dst += dst_stride;
299
4.20M
  }
300
96.0k
}
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
937k
                                   int sstep) {
309
937k
  const __m256i zero_reg = _mm256_setzero_si256();
310
937k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
311
937k
  int i;
312
41.5M
  for (i = 0; i < height; i++) {
313
40.6M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
314
40.6M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
315
40.6M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + sstep));
316
40.6M
    const __m256i src_avg = _mm256_avg_epu8(src_0, src_1);
317
40.6M
    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
40.6M
    } else {
324
40.6M
      exp_src_lo = _mm256_unpacklo_epi8(src_avg, zero_reg);
325
40.6M
      exp_src_hi = _mm256_unpackhi_epi8(src_avg, zero_reg);
326
40.6M
    }
327
40.6M
    CALC_SUM_SSE_INSIDE_LOOP
328
40.6M
    src += src_stride;
329
40.6M
    dst += dst_stride;
330
40.6M
  }
331
937k
}
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
470k
                               __m256i *sse_reg) {
338
470k
  spv32_half_zero(src, src_stride, dst, dst_stride, second_pred, second_stride,
339
470k
                  do_sec, height, sum_reg, sse_reg, src_stride);
340
470k
}
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
466k
                               __m256i *sse_reg) {
347
466k
  spv32_half_zero(src, src_stride, dst, dst_stride, second_pred, second_stride,
348
466k
                  do_sec, height, sum_reg, sse_reg, 1);
349
466k
}
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
280k
                               __m256i *sse_reg) {
356
280k
  const __m256i zero_reg = _mm256_setzero_si256();
357
280k
  const __m256i src_a = _mm256_loadu_si256((__m256i const *)src);
358
280k
  const __m256i src_b = _mm256_loadu_si256((__m256i const *)(src + 1));
359
280k
  __m256i prev_src_avg = _mm256_avg_epu8(src_a, src_b);
360
280k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
361
280k
  int i;
362
280k
  src += src_stride;
363
12.2M
  for (i = 0; i < height; i++) {
364
12.0M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
365
12.0M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)(src));
366
12.0M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + 1));
367
12.0M
    const __m256i src_avg = _mm256_avg_epu8(src_0, src_1);
368
12.0M
    const __m256i current_avg = _mm256_avg_epu8(prev_src_avg, src_avg);
369
12.0M
    prev_src_avg = src_avg;
370
371
12.0M
    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.0M
    } else {
378
12.0M
      exp_src_lo = _mm256_unpacklo_epi8(current_avg, zero_reg);
379
12.0M
      exp_src_hi = _mm256_unpackhi_epi8(current_avg, zero_reg);
380
12.0M
    }
381
    // save current source average
382
12.0M
    CALC_SUM_SSE_INSIDE_LOOP
383
12.0M
    dst += dst_stride;
384
12.0M
    src += src_stride;
385
12.0M
  }
386
280k
}
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
830k
                                    int offset, int sstep) {
395
830k
  const __m256i zero_reg = _mm256_setzero_si256();
396
830k
  const __m256i pw8 = _mm256_set1_epi16(8);
397
830k
  const __m256i filter = _mm256_load_si256(
398
830k
      (__m256i const *)(bilinear_filters_avx2 + (offset << 5)));
399
830k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
400
830k
  int i;
401
36.3M
  for (i = 0; i < height; i++) {
402
35.4M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
403
35.4M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
404
35.4M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + sstep));
405
35.4M
    exp_src_lo = _mm256_unpacklo_epi8(src_0, src_1);
406
35.4M
    exp_src_hi = _mm256_unpackhi_epi8(src_0, src_1);
407
408
35.4M
    FILTER_SRC(filter)
409
35.4M
    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.4M
    CALC_SUM_SSE_INSIDE_LOOP
418
35.4M
    src += src_stride;
419
35.4M
    dst += dst_stride;
420
35.4M
  }
421
830k
}
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
428k
                               __m256i *sse_reg, int y_offset) {
428
428k
  spv32_bilin_zero(src, src_stride, dst, dst_stride, second_pred, second_stride,
429
428k
                   do_sec, height, sum_reg, sse_reg, y_offset, src_stride);
430
428k
}
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
402k
                               __m256i *sse_reg, int x_offset) {
437
402k
  spv32_bilin_zero(src, src_stride, dst, dst_stride, second_pred, second_stride,
438
402k
                   do_sec, height, sum_reg, sse_reg, x_offset, 1);
439
402k
}
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.54M
  for (i = 0; i < height; i++) {
457
6.39M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
458
6.39M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
459
6.39M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + 1));
460
6.39M
    const __m256i src_avg = _mm256_avg_epu8(src_0, src_1);
461
6.39M
    exp_src_lo = _mm256_unpacklo_epi8(prev_src_avg, src_avg);
462
6.39M
    exp_src_hi = _mm256_unpackhi_epi8(prev_src_avg, src_avg);
463
6.39M
    prev_src_avg = src_avg;
464
465
6.39M
    FILTER_SRC(filter)
466
6.39M
    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.39M
    CALC_SUM_SSE_INSIDE_LOOP
475
6.39M
    dst += dst_stride;
476
6.39M
    src += src_stride;
477
6.39M
  }
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
162k
                               __m256i *sse_reg, int x_offset) {
485
162k
  const __m256i zero_reg = _mm256_setzero_si256();
486
162k
  const __m256i pw8 = _mm256_set1_epi16(8);
487
162k
  const __m256i filter = _mm256_load_si256(
488
162k
      (__m256i const *)(bilinear_filters_avx2 + (x_offset << 5)));
489
162k
  const __m256i src_a = _mm256_loadu_si256((__m256i const *)src);
490
162k
  const __m256i src_b = _mm256_loadu_si256((__m256i const *)(src + 1));
491
162k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
492
162k
  __m256i src_reg, src_pack;
493
162k
  int i;
494
162k
  exp_src_lo = _mm256_unpacklo_epi8(src_a, src_b);
495
162k
  exp_src_hi = _mm256_unpackhi_epi8(src_a, src_b);
496
162k
  FILTER_SRC(filter)
497
  // convert each 16 bit to 8 bit to each low and high lane source
498
162k
  src_pack = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
499
500
162k
  src += src_stride;
501
7.24M
  for (i = 0; i < height; i++) {
502
7.08M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
503
7.08M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
504
7.08M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + 1));
505
7.08M
    exp_src_lo = _mm256_unpacklo_epi8(src_0, src_1);
506
7.08M
    exp_src_hi = _mm256_unpackhi_epi8(src_0, src_1);
507
508
7.08M
    FILTER_SRC(filter)
509
510
7.08M
    src_reg = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
511
    // average between previous pack to the current
512
7.08M
    src_pack = _mm256_avg_epu8(src_pack, src_reg);
513
514
7.08M
    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.08M
    } else {
521
7.08M
      exp_src_lo = _mm256_unpacklo_epi8(src_pack, zero_reg);
522
7.08M
      exp_src_hi = _mm256_unpackhi_epi8(src_pack, zero_reg);
523
7.08M
    }
524
7.08M
    CALC_SUM_SSE_INSIDE_LOOP
525
7.08M
    src_pack = src_reg;
526
7.08M
    dst += dst_stride;
527
7.08M
    src += src_stride;
528
7.08M
  }
529
162k
}
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
409k
                               __m256i *sse_reg, int x_offset, int y_offset) {
536
409k
  const __m256i zero_reg = _mm256_setzero_si256();
537
409k
  const __m256i pw8 = _mm256_set1_epi16(8);
538
409k
  const __m256i xfilter = _mm256_load_si256(
539
409k
      (__m256i const *)(bilinear_filters_avx2 + (x_offset << 5)));
540
409k
  const __m256i yfilter = _mm256_load_si256(
541
409k
      (__m256i const *)(bilinear_filters_avx2 + (y_offset << 5)));
542
409k
  const __m256i src_a = _mm256_loadu_si256((__m256i const *)src);
543
409k
  const __m256i src_b = _mm256_loadu_si256((__m256i const *)(src + 1));
544
409k
  __m256i exp_src_lo, exp_src_hi, exp_dst_lo, exp_dst_hi;
545
409k
  __m256i prev_src_pack, src_pack;
546
409k
  int i;
547
409k
  exp_src_lo = _mm256_unpacklo_epi8(src_a, src_b);
548
409k
  exp_src_hi = _mm256_unpackhi_epi8(src_a, src_b);
549
409k
  FILTER_SRC(xfilter)
550
  // convert each 16 bit to 8 bit to each low and high lane source
551
409k
  prev_src_pack = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
552
409k
  src += src_stride;
553
554
17.9M
  for (i = 0; i < height; i++) {
555
17.5M
    const __m256i dst_reg = _mm256_loadu_si256((__m256i const *)dst);
556
17.5M
    const __m256i src_0 = _mm256_loadu_si256((__m256i const *)src);
557
17.5M
    const __m256i src_1 = _mm256_loadu_si256((__m256i const *)(src + 1));
558
17.5M
    exp_src_lo = _mm256_unpacklo_epi8(src_0, src_1);
559
17.5M
    exp_src_hi = _mm256_unpackhi_epi8(src_0, src_1);
560
561
17.5M
    FILTER_SRC(xfilter)
562
17.5M
    src_pack = _mm256_packus_epi16(exp_src_lo, exp_src_hi);
563
564
    // merge previous pack to current pack source
565
17.5M
    exp_src_lo = _mm256_unpacklo_epi8(prev_src_pack, src_pack);
566
17.5M
    exp_src_hi = _mm256_unpackhi_epi8(prev_src_pack, src_pack);
567
568
17.5M
    FILTER_SRC(yfilter)
569
17.5M
    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.5M
    prev_src_pack = src_pack;
579
580
17.5M
    CALC_SUM_SSE_INSIDE_LOOP
581
17.5M
    dst += dst_stride;
582
17.5M
    src += src_stride;
583
17.5M
  }
584
409k
}
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.86M
                                  int do_sec, int height, unsigned int *sse) {
591
2.86M
  const __m256i zero_reg = _mm256_setzero_si256();
592
2.86M
  __m256i sum_reg = _mm256_setzero_si256();
593
2.86M
  __m256i sse_reg = _mm256_setzero_si256();
594
2.86M
  __m256i sse_reg_hi, res_cmp, sum_reg_lo, sum_reg_hi;
595
2.86M
  int sum;
596
  // x_offset = 0 and y_offset = 0
597
2.86M
  if (x_offset == 0) {
598
995k
    if (y_offset == 0) {
599
96.0k
      spv32_x0_y0(src, src_stride, dst, dst_stride, second_pred, second_stride,
600
96.0k
                  do_sec, height, &sum_reg, &sse_reg);
601
      // x_offset = 0 and y_offset = 4
602
899k
    } else if (y_offset == 4) {
603
470k
      spv32_x0_y4(src, src_stride, dst, dst_stride, second_pred, second_stride,
604
470k
                  do_sec, height, &sum_reg, &sse_reg);
605
      // x_offset = 0 and y_offset = bilin interpolation
606
470k
    } else {
607
428k
      spv32_x0_yb(src, src_stride, dst, dst_stride, second_pred, second_stride,
608
428k
                  do_sec, height, &sum_reg, &sse_reg, y_offset);
609
428k
    }
610
    // x_offset = 4  and y_offset = 0
611
1.86M
  } else if (x_offset == 4) {
612
893k
    if (y_offset == 0) {
613
466k
      spv32_x4_y0(src, src_stride, dst, dst_stride, second_pred, second_stride,
614
466k
                  do_sec, height, &sum_reg, &sse_reg);
615
      // x_offset = 4  and y_offset = 4
616
466k
    } else if (y_offset == 4) {
617
280k
      spv32_x4_y4(src, src_stride, dst, dst_stride, second_pred, second_stride,
618
280k
                  do_sec, height, &sum_reg, &sse_reg);
619
      // x_offset = 4  and y_offset = bilin interpolation
620
280k
    } 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
974k
  } else {
626
974k
    if (y_offset == 0) {
627
402k
      spv32_xb_y0(src, src_stride, dst, dst_stride, second_pred, second_stride,
628
402k
                  do_sec, height, &sum_reg, &sse_reg, x_offset);
629
      // x_offset = bilin interpolation and y_offset = 4
630
572k
    } else if (y_offset == 4) {
631
162k
      spv32_xb_y4(src, src_stride, dst, dst_stride, second_pred, second_stride,
632
162k
                  do_sec, height, &sum_reg, &sse_reg, x_offset);
633
      // x_offset = bilin interpolation and y_offset = bilin interpolation
634
409k
    } else {
635
409k
      spv32_xb_yb(src, src_stride, dst, dst_stride, second_pred, second_stride,
636
409k
                  do_sec, height, &sum_reg, &sse_reg, x_offset, y_offset);
637
409k
    }
638
974k
  }
639
2.86M
  CALC_SUM_AND_SSE
640
2.86M
  return sum;
641
2.86M
}
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.86M
                                       int height, unsigned int *sse) {
647
2.86M
  return sub_pix_var32xh(src, src_stride, x_offset, y_offset, dst, dst_stride,
648
2.86M
                         NULL, 0, 0, height, sse);
649
2.86M
}
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.9M
                                  unsigned int *sse) {
668
10.9M
  __m256i vsse, vsum;
669
10.9M
  int sum;
670
10.9M
  variance8_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 4, &vsse, &vsum);
671
10.9M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
672
10.9M
  return *sse - ((sum * sum) >> 5);
673
10.9M
}
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
145M
                                  unsigned int *sse) {
678
145M
  __m256i vsse, vsum;
679
145M
  int sum;
680
145M
  variance8_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 8, &vsse, &vsum);
681
145M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
682
145M
  return *sse - ((sum * sum) >> 6);
683
145M
}
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.26M
                                   unsigned int *sse) {
688
8.26M
  __m256i vsse, vsum;
689
8.26M
  int sum;
690
8.26M
  variance8_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
691
8.26M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
692
8.26M
  return *sse - ((sum * sum) >> 7);
693
8.26M
}
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.18M
                                   unsigned int *sse) {
698
8.18M
  int sum;
699
8.18M
  __m256i vsse, vsum;
700
8.18M
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 8, &vsse, &vsum);
701
8.18M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
702
8.18M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 7);
703
8.18M
}
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
42.8M
                                    unsigned int *sse) {
708
42.8M
  int sum;
709
42.8M
  __m256i vsse, vsum;
710
42.8M
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
711
42.8M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
712
42.8M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 8);
713
42.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.86M
                                    unsigned int *sse) {
718
1.86M
  int sum;
719
1.86M
  __m256i vsse, vsum;
720
1.86M
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 32, &vsse, &vsum);
721
1.86M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
722
1.86M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 9);
723
1.86M
}
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.12M
                                    unsigned int *sse) {
728
2.12M
  int sum;
729
2.12M
  __m256i vsse, vsum;
730
2.12M
  variance32_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
731
2.12M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
732
2.12M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 9);
733
2.12M
}
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.75M
                                    unsigned int *sse) {
738
7.75M
  int sum;
739
7.75M
  __m256i vsse, vsum;
740
7.75M
  __m128i vsum_128;
741
7.75M
  variance32_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 32, &vsse, &vsum);
742
7.75M
  vsum_128 = _mm_add_epi16(_mm256_castsi256_si128(vsum),
743
7.75M
                           _mm256_extractf128_si256(vsum, 1));
744
7.75M
  vsum_128 = _mm_add_epi32(_mm_cvtepi16_epi32(vsum_128),
745
7.75M
                           _mm_cvtepi16_epi32(_mm_srli_si128(vsum_128, 8)));
746
7.75M
  variance_final_from_32bit_sum_avx2(vsse, vsum_128, sse, &sum);
747
7.75M
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 10);
748
7.75M
}
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
372k
                                    unsigned int *sse) {
753
372k
  int sum;
754
372k
  __m256i vsse, vsum;
755
372k
  __m128i vsum_128;
756
372k
  variance32_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 64, &vsse, &vsum);
757
372k
  vsum = sum_to_32bit_avx2(vsum);
758
372k
  vsum_128 = _mm_add_epi32(_mm256_castsi256_si128(vsum),
759
372k
                           _mm256_extractf128_si256(vsum, 1));
760
372k
  variance_final_from_32bit_sum_avx2(vsse, vsum_128, sse, &sum);
761
372k
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 11);
762
372k
}
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
622k
                                    unsigned int *sse) {
767
622k
  __m256i vsse = _mm256_setzero_si256();
768
622k
  __m256i vsum = _mm256_setzero_si256();
769
622k
  __m128i vsum_128;
770
622k
  int sum;
771
622k
  variance64_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 32, &vsse, &vsum);
772
622k
  vsum = sum_to_32bit_avx2(vsum);
773
622k
  vsum_128 = _mm_add_epi32(_mm256_castsi256_si128(vsum),
774
622k
                           _mm256_extractf128_si256(vsum, 1));
775
622k
  variance_final_from_32bit_sum_avx2(vsse, vsum_128, sse, &sum);
776
622k
  return *sse - (uint32_t)(((int64_t)sum * sum) >> 11);
777
622k
}
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
639k
                                    unsigned int *sse) {
782
639k
  __m256i vsse = _mm256_setzero_si256();
783
639k
  __m256i vsum = _mm256_setzero_si256();
784
639k
  __m128i vsum_128;
785
639k
  int sum;
786
639k
  int i = 0;
787
788
1.91M
  for (i = 0; i < 2; i++) {
789
1.27M
    __m256i vsum16;
790
1.27M
    variance64_avx2(src_ptr + 32 * i * src_stride, src_stride,
791
1.27M
                    ref_ptr + 32 * i * ref_stride, ref_stride, 32, &vsse,
792
1.27M
                    &vsum16);
793
1.27M
    vsum = _mm256_add_epi32(vsum, sum_to_32bit_avx2(vsum16));
794
1.27M
  }
795
639k
  vsum_128 = _mm_add_epi32(_mm256_castsi256_si128(vsum),
796
639k
                           _mm256_extractf128_si256(vsum, 1));
797
639k
  variance_final_from_32bit_sum_avx2(vsse, vsum_128, sse, &sum);
798
639k
  return *sse - (unsigned int)(((int64_t)sum * sum) >> 12);
799
639k
}
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.2M
                               unsigned int *sse) {
814
12.2M
  int sum;
815
12.2M
  __m256i vsse, vsum;
816
12.2M
  variance16_avx2(src_ptr, src_stride, ref_ptr, ref_stride, 16, &vsse, &vsum);
817
12.2M
  variance_final_from_16bit_sum_avx2(vsse, vsum, sse, &sum);
818
12.2M
  return *sse;
819
12.2M
}
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
495k
    const uint8_t *ref_ptr, int ref_stride, unsigned int *sse) {
824
495k
  unsigned int sse1;
825
495k
  const int se1 = sub_pixel_variance32xh_avx2(
826
495k
      src_ptr, src_stride, x_offset, y_offset, ref_ptr, ref_stride, 64, &sse1);
827
495k
  unsigned int sse2;
828
495k
  const int se2 =
829
495k
      sub_pixel_variance32xh_avx2(src_ptr + 32, src_stride, x_offset, y_offset,
830
495k
                                  ref_ptr + 32, ref_stride, 64, &sse2);
831
495k
  const int se = se1 + se2;
832
495k
  *sse = sse1 + sse2;
833
495k
  return *sse - (uint32_t)(((int64_t)se * se) >> 12);
834
495k
}
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.87M
    const uint8_t *ref_ptr, int ref_stride, unsigned int *sse) {
839
1.87M
  const int se = sub_pixel_variance32xh_avx2(
840
1.87M
      src_ptr, src_stride, x_offset, y_offset, ref_ptr, ref_stride, 32, sse);
841
1.87M
  return *sse - (uint32_t)(((int64_t)se * se) >> 10);
842
1.87M
}
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
}