1*77c1e3ccSAndroid Build Coastguard Worker /*
2*77c1e3ccSAndroid Build Coastguard Worker * Copyright (c) 2018, Alliance for Open Media. All rights reserved.
3*77c1e3ccSAndroid Build Coastguard Worker *
4*77c1e3ccSAndroid Build Coastguard Worker * This source code is subject to the terms of the BSD 2 Clause License and
5*77c1e3ccSAndroid Build Coastguard Worker * the Alliance for Open Media Patent License 1.0. If the BSD 2 Clause License
6*77c1e3ccSAndroid Build Coastguard Worker * was not distributed with this source code in the LICENSE file, you can
7*77c1e3ccSAndroid Build Coastguard Worker * obtain it at www.aomedia.org/license/software. If the Alliance for Open
8*77c1e3ccSAndroid Build Coastguard Worker * Media Patent License 1.0 was not distributed with this source code in the
9*77c1e3ccSAndroid Build Coastguard Worker * PATENTS file, you can obtain it at www.aomedia.org/license/patent.
10*77c1e3ccSAndroid Build Coastguard Worker */
11*77c1e3ccSAndroid Build Coastguard Worker
12*77c1e3ccSAndroid Build Coastguard Worker #ifndef AOM_AOM_DSP_X86_CONVOLVE_AVX2_H_
13*77c1e3ccSAndroid Build Coastguard Worker #define AOM_AOM_DSP_X86_CONVOLVE_AVX2_H_
14*77c1e3ccSAndroid Build Coastguard Worker
15*77c1e3ccSAndroid Build Coastguard Worker #include <immintrin.h>
16*77c1e3ccSAndroid Build Coastguard Worker
17*77c1e3ccSAndroid Build Coastguard Worker #include "aom_ports/mem.h"
18*77c1e3ccSAndroid Build Coastguard Worker
19*77c1e3ccSAndroid Build Coastguard Worker #include "av1/common/convolve.h"
20*77c1e3ccSAndroid Build Coastguard Worker #include "av1/common/filter.h"
21*77c1e3ccSAndroid Build Coastguard Worker
22*77c1e3ccSAndroid Build Coastguard Worker // filters for 16
23*77c1e3ccSAndroid Build Coastguard Worker DECLARE_ALIGNED(32, static const uint8_t, filt_global_avx2[]) = {
24*77c1e3ccSAndroid Build Coastguard Worker 0, 1, 1, 2, 2, 3, 3, 4, 4, 5, 5, 6, 6, 7, 7, 8, 0, 1, 1,
25*77c1e3ccSAndroid Build Coastguard Worker 2, 2, 3, 3, 4, 4, 5, 5, 6, 6, 7, 7, 8, 2, 3, 3, 4, 4, 5,
26*77c1e3ccSAndroid Build Coastguard Worker 5, 6, 6, 7, 7, 8, 8, 9, 9, 10, 2, 3, 3, 4, 4, 5, 5, 6, 6,
27*77c1e3ccSAndroid Build Coastguard Worker 7, 7, 8, 8, 9, 9, 10, 4, 5, 5, 6, 6, 7, 7, 8, 8, 9, 9, 10,
28*77c1e3ccSAndroid Build Coastguard Worker 10, 11, 11, 12, 4, 5, 5, 6, 6, 7, 7, 8, 8, 9, 9, 10, 10, 11, 11,
29*77c1e3ccSAndroid Build Coastguard Worker 12, 6, 7, 7, 8, 8, 9, 9, 10, 10, 11, 11, 12, 12, 13, 13, 14, 6, 7,
30*77c1e3ccSAndroid Build Coastguard Worker 7, 8, 8, 9, 9, 10, 10, 11, 11, 12, 12, 13, 13, 14
31*77c1e3ccSAndroid Build Coastguard Worker };
32*77c1e3ccSAndroid Build Coastguard Worker
33*77c1e3ccSAndroid Build Coastguard Worker DECLARE_ALIGNED(32, static const uint8_t, filt_d4_global_avx2[]) = {
34*77c1e3ccSAndroid Build Coastguard Worker 0, 1, 2, 3, 1, 2, 3, 4, 2, 3, 4, 5, 3, 4, 5, 6, 0, 1, 2, 3, 1, 2,
35*77c1e3ccSAndroid Build Coastguard Worker 3, 4, 2, 3, 4, 5, 3, 4, 5, 6, 4, 5, 6, 7, 5, 6, 7, 8, 6, 7, 8, 9,
36*77c1e3ccSAndroid Build Coastguard Worker 7, 8, 9, 10, 4, 5, 6, 7, 5, 6, 7, 8, 6, 7, 8, 9, 7, 8, 9, 10,
37*77c1e3ccSAndroid Build Coastguard Worker };
38*77c1e3ccSAndroid Build Coastguard Worker
39*77c1e3ccSAndroid Build Coastguard Worker DECLARE_ALIGNED(32, static const uint8_t, filt4_d4_global_avx2[]) = {
40*77c1e3ccSAndroid Build Coastguard Worker 2, 3, 4, 5, 3, 4, 5, 6, 4, 5, 6, 7, 5, 6, 7, 8,
41*77c1e3ccSAndroid Build Coastguard Worker 2, 3, 4, 5, 3, 4, 5, 6, 4, 5, 6, 7, 5, 6, 7, 8,
42*77c1e3ccSAndroid Build Coastguard Worker };
43*77c1e3ccSAndroid Build Coastguard Worker
44*77c1e3ccSAndroid Build Coastguard Worker DECLARE_ALIGNED(32, static const uint8_t, filt_center_global_avx2[32]) = {
45*77c1e3ccSAndroid Build Coastguard Worker 3, 255, 4, 255, 5, 255, 6, 255, 7, 255, 8, 255, 9, 255, 10, 255,
46*77c1e3ccSAndroid Build Coastguard Worker 3, 255, 4, 255, 5, 255, 6, 255, 7, 255, 8, 255, 9, 255, 10, 255
47*77c1e3ccSAndroid Build Coastguard Worker };
48*77c1e3ccSAndroid Build Coastguard Worker
49*77c1e3ccSAndroid Build Coastguard Worker DECLARE_ALIGNED(32, static const uint8_t,
50*77c1e3ccSAndroid Build Coastguard Worker filt1_global_avx2[32]) = { 0, 1, 1, 2, 2, 3, 3, 4, 4, 5, 5,
51*77c1e3ccSAndroid Build Coastguard Worker 6, 6, 7, 7, 8, 0, 1, 1, 2, 2, 3,
52*77c1e3ccSAndroid Build Coastguard Worker 3, 4, 4, 5, 5, 6, 6, 7, 7, 8 };
53*77c1e3ccSAndroid Build Coastguard Worker
54*77c1e3ccSAndroid Build Coastguard Worker DECLARE_ALIGNED(32, static const uint8_t,
55*77c1e3ccSAndroid Build Coastguard Worker filt2_global_avx2[32]) = { 2, 3, 3, 4, 4, 5, 5, 6, 6, 7, 7,
56*77c1e3ccSAndroid Build Coastguard Worker 8, 8, 9, 9, 10, 2, 3, 3, 4, 4, 5,
57*77c1e3ccSAndroid Build Coastguard Worker 5, 6, 6, 7, 7, 8, 8, 9, 9, 10 };
58*77c1e3ccSAndroid Build Coastguard Worker
59*77c1e3ccSAndroid Build Coastguard Worker DECLARE_ALIGNED(32, static const uint8_t, filt3_global_avx2[32]) = {
60*77c1e3ccSAndroid Build Coastguard Worker 4, 5, 5, 6, 6, 7, 7, 8, 8, 9, 9, 10, 10, 11, 11, 12,
61*77c1e3ccSAndroid Build Coastguard Worker 4, 5, 5, 6, 6, 7, 7, 8, 8, 9, 9, 10, 10, 11, 11, 12
62*77c1e3ccSAndroid Build Coastguard Worker };
63*77c1e3ccSAndroid Build Coastguard Worker
64*77c1e3ccSAndroid Build Coastguard Worker DECLARE_ALIGNED(32, static const uint8_t, filt4_global_avx2[32]) = {
65*77c1e3ccSAndroid Build Coastguard Worker 6, 7, 7, 8, 8, 9, 9, 10, 10, 11, 11, 12, 12, 13, 13, 14,
66*77c1e3ccSAndroid Build Coastguard Worker 6, 7, 7, 8, 8, 9, 9, 10, 10, 11, 11, 12, 12, 13, 13, 14
67*77c1e3ccSAndroid Build Coastguard Worker };
68*77c1e3ccSAndroid Build Coastguard Worker
69*77c1e3ccSAndroid Build Coastguard Worker #define CONVOLVE_SR_HORIZONTAL_FILTER_4TAP \
70*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < (im_h - 2); i += 2) { \
71*77c1e3ccSAndroid Build Coastguard Worker __m256i data = _mm256_castsi128_si256( \
72*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)&src_ptr[(i * src_stride) + j])); \
73*77c1e3ccSAndroid Build Coastguard Worker data = _mm256_inserti128_si256( \
74*77c1e3ccSAndroid Build Coastguard Worker data, \
75*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128( \
76*77c1e3ccSAndroid Build Coastguard Worker (__m128i *)&src_ptr[(i * src_stride) + j + src_stride]), \
77*77c1e3ccSAndroid Build Coastguard Worker 1); \
78*77c1e3ccSAndroid Build Coastguard Worker __m256i res = convolve_lowbd_x_4tap(data, coeffs_h + 1, filt); \
79*77c1e3ccSAndroid Build Coastguard Worker res = \
80*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi16(_mm256_add_epi16(res, round_const_h), round_shift_h); \
81*77c1e3ccSAndroid Build Coastguard Worker _mm256_store_si256((__m256i *)&im_block[i * im_stride], res); \
82*77c1e3ccSAndroid Build Coastguard Worker } \
83*77c1e3ccSAndroid Build Coastguard Worker __m256i data_1 = _mm256_castsi128_si256( \
84*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)&src_ptr[(i * src_stride) + j])); \
85*77c1e3ccSAndroid Build Coastguard Worker __m256i res = convolve_lowbd_x_4tap(data_1, coeffs_h + 1, filt); \
86*77c1e3ccSAndroid Build Coastguard Worker res = _mm256_sra_epi16(_mm256_add_epi16(res, round_const_h), round_shift_h); \
87*77c1e3ccSAndroid Build Coastguard Worker _mm256_store_si256((__m256i *)&im_block[i * im_stride], res);
88*77c1e3ccSAndroid Build Coastguard Worker
89*77c1e3ccSAndroid Build Coastguard Worker #define CONVOLVE_SR_VERTICAL_FILTER_4TAP \
90*77c1e3ccSAndroid Build Coastguard Worker __m256i s[6]; \
91*77c1e3ccSAndroid Build Coastguard Worker __m256i src_0 = _mm256_loadu_si256((__m256i *)(im_block + 0 * im_stride)); \
92*77c1e3ccSAndroid Build Coastguard Worker __m256i src_1 = _mm256_loadu_si256((__m256i *)(im_block + 1 * im_stride)); \
93*77c1e3ccSAndroid Build Coastguard Worker __m256i src_2 = _mm256_loadu_si256((__m256i *)(im_block + 2 * im_stride)); \
94*77c1e3ccSAndroid Build Coastguard Worker __m256i src_3 = _mm256_loadu_si256((__m256i *)(im_block + 3 * im_stride)); \
95*77c1e3ccSAndroid Build Coastguard Worker \
96*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_unpacklo_epi16(src_0, src_1); \
97*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_unpacklo_epi16(src_2, src_3); \
98*77c1e3ccSAndroid Build Coastguard Worker s[3] = _mm256_unpackhi_epi16(src_0, src_1); \
99*77c1e3ccSAndroid Build Coastguard Worker s[4] = _mm256_unpackhi_epi16(src_2, src_3); \
100*77c1e3ccSAndroid Build Coastguard Worker \
101*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < h; i += 2) { \
102*77c1e3ccSAndroid Build Coastguard Worker const int16_t *data = &im_block[i * im_stride]; \
103*77c1e3ccSAndroid Build Coastguard Worker const __m256i s4 = _mm256_loadu_si256((__m256i *)(data + 4 * im_stride)); \
104*77c1e3ccSAndroid Build Coastguard Worker const __m256i s5 = _mm256_loadu_si256((__m256i *)(data + 5 * im_stride)); \
105*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_unpacklo_epi16(s4, s5); \
106*77c1e3ccSAndroid Build Coastguard Worker s[5] = _mm256_unpackhi_epi16(s4, s5); \
107*77c1e3ccSAndroid Build Coastguard Worker \
108*77c1e3ccSAndroid Build Coastguard Worker __m256i res_a = convolve_4tap(s, coeffs_v + 1); \
109*77c1e3ccSAndroid Build Coastguard Worker __m256i res_b = convolve_4tap(s + 3, coeffs_v + 1); \
110*77c1e3ccSAndroid Build Coastguard Worker \
111*77c1e3ccSAndroid Build Coastguard Worker res_a = \
112*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi32(_mm256_add_epi32(res_a, sum_round_v), sum_shift_v); \
113*77c1e3ccSAndroid Build Coastguard Worker res_b = \
114*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi32(_mm256_add_epi32(res_b, sum_round_v), sum_shift_v); \
115*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_a_round = _mm256_sra_epi32( \
116*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_a, round_const_v), round_shift_v); \
117*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_b_round = _mm256_sra_epi32( \
118*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_b, round_const_v), round_shift_v); \
119*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_16bit = _mm256_packs_epi32(res_a_round, res_b_round); \
120*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_8b = _mm256_packus_epi16(res_16bit, res_16bit); \
121*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_castsi256_si128(res_8b); \
122*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_8b, 1); \
123*77c1e3ccSAndroid Build Coastguard Worker \
124*77c1e3ccSAndroid Build Coastguard Worker __m128i *const p_0 = (__m128i *)&dst[i * dst_stride + j]; \
125*77c1e3ccSAndroid Build Coastguard Worker __m128i *const p_1 = (__m128i *)&dst[i * dst_stride + j + dst_stride]; \
126*77c1e3ccSAndroid Build Coastguard Worker if (w - j > 4) { \
127*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64(p_0, res_0); \
128*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64(p_1, res_1); \
129*77c1e3ccSAndroid Build Coastguard Worker } else if (w == 4) { \
130*77c1e3ccSAndroid Build Coastguard Worker xx_storel_32(p_0, res_0); \
131*77c1e3ccSAndroid Build Coastguard Worker xx_storel_32(p_1, res_1); \
132*77c1e3ccSAndroid Build Coastguard Worker } else { \
133*77c1e3ccSAndroid Build Coastguard Worker *(uint16_t *)p_0 = (uint16_t)_mm_cvtsi128_si32(res_0); \
134*77c1e3ccSAndroid Build Coastguard Worker *(uint16_t *)p_1 = (uint16_t)_mm_cvtsi128_si32(res_1); \
135*77c1e3ccSAndroid Build Coastguard Worker } \
136*77c1e3ccSAndroid Build Coastguard Worker \
137*77c1e3ccSAndroid Build Coastguard Worker s[0] = s[1]; \
138*77c1e3ccSAndroid Build Coastguard Worker s[1] = s[2]; \
139*77c1e3ccSAndroid Build Coastguard Worker s[3] = s[4]; \
140*77c1e3ccSAndroid Build Coastguard Worker s[4] = s[5]; \
141*77c1e3ccSAndroid Build Coastguard Worker }
142*77c1e3ccSAndroid Build Coastguard Worker
143*77c1e3ccSAndroid Build Coastguard Worker #define CONVOLVE_SR_HORIZONTAL_FILTER_6TAP \
144*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < (im_h - 2); i += 2) { \
145*77c1e3ccSAndroid Build Coastguard Worker __m256i data = _mm256_castsi128_si256( \
146*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)&src_ptr[(i * src_stride) + j])); \
147*77c1e3ccSAndroid Build Coastguard Worker data = _mm256_inserti128_si256( \
148*77c1e3ccSAndroid Build Coastguard Worker data, \
149*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128( \
150*77c1e3ccSAndroid Build Coastguard Worker (__m128i *)&src_ptr[(i * src_stride) + j + src_stride]), \
151*77c1e3ccSAndroid Build Coastguard Worker 1); \
152*77c1e3ccSAndroid Build Coastguard Worker \
153*77c1e3ccSAndroid Build Coastguard Worker __m256i res = convolve_lowbd_x_6tap(data, coeffs_h, filt); \
154*77c1e3ccSAndroid Build Coastguard Worker res = \
155*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi16(_mm256_add_epi16(res, round_const_h), round_shift_h); \
156*77c1e3ccSAndroid Build Coastguard Worker _mm256_store_si256((__m256i *)&im_block[i * im_stride], res); \
157*77c1e3ccSAndroid Build Coastguard Worker } \
158*77c1e3ccSAndroid Build Coastguard Worker \
159*77c1e3ccSAndroid Build Coastguard Worker __m256i data_1 = _mm256_castsi128_si256( \
160*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)&src_ptr[(i * src_stride) + j])); \
161*77c1e3ccSAndroid Build Coastguard Worker \
162*77c1e3ccSAndroid Build Coastguard Worker __m256i res = convolve_lowbd_x_6tap(data_1, coeffs_h, filt); \
163*77c1e3ccSAndroid Build Coastguard Worker \
164*77c1e3ccSAndroid Build Coastguard Worker res = _mm256_sra_epi16(_mm256_add_epi16(res, round_const_h), round_shift_h); \
165*77c1e3ccSAndroid Build Coastguard Worker \
166*77c1e3ccSAndroid Build Coastguard Worker _mm256_store_si256((__m256i *)&im_block[i * im_stride], res);
167*77c1e3ccSAndroid Build Coastguard Worker
168*77c1e3ccSAndroid Build Coastguard Worker #define CONVOLVE_SR_VERTICAL_FILTER_6TAP \
169*77c1e3ccSAndroid Build Coastguard Worker __m256i src_0 = _mm256_loadu_si256((__m256i *)(im_block + 0 * im_stride)); \
170*77c1e3ccSAndroid Build Coastguard Worker __m256i src_1 = _mm256_loadu_si256((__m256i *)(im_block + 1 * im_stride)); \
171*77c1e3ccSAndroid Build Coastguard Worker __m256i src_2 = _mm256_loadu_si256((__m256i *)(im_block + 2 * im_stride)); \
172*77c1e3ccSAndroid Build Coastguard Worker __m256i src_3 = _mm256_loadu_si256((__m256i *)(im_block + 3 * im_stride)); \
173*77c1e3ccSAndroid Build Coastguard Worker \
174*77c1e3ccSAndroid Build Coastguard Worker __m256i s[8]; \
175*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_unpacklo_epi16(src_0, src_1); \
176*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_unpacklo_epi16(src_2, src_3); \
177*77c1e3ccSAndroid Build Coastguard Worker \
178*77c1e3ccSAndroid Build Coastguard Worker s[3] = _mm256_unpackhi_epi16(src_0, src_1); \
179*77c1e3ccSAndroid Build Coastguard Worker s[4] = _mm256_unpackhi_epi16(src_2, src_3); \
180*77c1e3ccSAndroid Build Coastguard Worker \
181*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < h; i += 2) { \
182*77c1e3ccSAndroid Build Coastguard Worker const int16_t *data = &im_block[i * im_stride]; \
183*77c1e3ccSAndroid Build Coastguard Worker \
184*77c1e3ccSAndroid Build Coastguard Worker const __m256i s6 = _mm256_loadu_si256((__m256i *)(data + 4 * im_stride)); \
185*77c1e3ccSAndroid Build Coastguard Worker const __m256i s7 = _mm256_loadu_si256((__m256i *)(data + 5 * im_stride)); \
186*77c1e3ccSAndroid Build Coastguard Worker \
187*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_unpacklo_epi16(s6, s7); \
188*77c1e3ccSAndroid Build Coastguard Worker s[5] = _mm256_unpackhi_epi16(s6, s7); \
189*77c1e3ccSAndroid Build Coastguard Worker \
190*77c1e3ccSAndroid Build Coastguard Worker __m256i res_a = convolve_6tap(s, coeffs_v); \
191*77c1e3ccSAndroid Build Coastguard Worker __m256i res_b = convolve_6tap(s + 3, coeffs_v); \
192*77c1e3ccSAndroid Build Coastguard Worker \
193*77c1e3ccSAndroid Build Coastguard Worker res_a = \
194*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi32(_mm256_add_epi32(res_a, sum_round_v), sum_shift_v); \
195*77c1e3ccSAndroid Build Coastguard Worker res_b = \
196*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi32(_mm256_add_epi32(res_b, sum_round_v), sum_shift_v); \
197*77c1e3ccSAndroid Build Coastguard Worker \
198*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_a_round = _mm256_sra_epi32( \
199*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_a, round_const_v), round_shift_v); \
200*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_b_round = _mm256_sra_epi32( \
201*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_b, round_const_v), round_shift_v); \
202*77c1e3ccSAndroid Build Coastguard Worker \
203*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_16bit = _mm256_packs_epi32(res_a_round, res_b_round); \
204*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_8b = _mm256_packus_epi16(res_16bit, res_16bit); \
205*77c1e3ccSAndroid Build Coastguard Worker \
206*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_castsi256_si128(res_8b); \
207*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_8b, 1); \
208*77c1e3ccSAndroid Build Coastguard Worker \
209*77c1e3ccSAndroid Build Coastguard Worker __m128i *const p_0 = (__m128i *)&dst[i * dst_stride + j]; \
210*77c1e3ccSAndroid Build Coastguard Worker __m128i *const p_1 = (__m128i *)&dst[i * dst_stride + j + dst_stride]; \
211*77c1e3ccSAndroid Build Coastguard Worker if (w - j > 4) { \
212*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64(p_0, res_0); \
213*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64(p_1, res_1); \
214*77c1e3ccSAndroid Build Coastguard Worker } else if (w == 4) { \
215*77c1e3ccSAndroid Build Coastguard Worker xx_storel_32(p_0, res_0); \
216*77c1e3ccSAndroid Build Coastguard Worker xx_storel_32(p_1, res_1); \
217*77c1e3ccSAndroid Build Coastguard Worker } else { \
218*77c1e3ccSAndroid Build Coastguard Worker *(uint16_t *)p_0 = (uint16_t)_mm_cvtsi128_si32(res_0); \
219*77c1e3ccSAndroid Build Coastguard Worker *(uint16_t *)p_1 = (uint16_t)_mm_cvtsi128_si32(res_1); \
220*77c1e3ccSAndroid Build Coastguard Worker } \
221*77c1e3ccSAndroid Build Coastguard Worker \
222*77c1e3ccSAndroid Build Coastguard Worker s[0] = s[1]; \
223*77c1e3ccSAndroid Build Coastguard Worker s[1] = s[2]; \
224*77c1e3ccSAndroid Build Coastguard Worker \
225*77c1e3ccSAndroid Build Coastguard Worker s[3] = s[4]; \
226*77c1e3ccSAndroid Build Coastguard Worker s[4] = s[5]; \
227*77c1e3ccSAndroid Build Coastguard Worker }
228*77c1e3ccSAndroid Build Coastguard Worker
229*77c1e3ccSAndroid Build Coastguard Worker #define CONVOLVE_SR_HORIZONTAL_FILTER_8TAP \
230*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < (im_h - 2); i += 2) { \
231*77c1e3ccSAndroid Build Coastguard Worker __m256i data = _mm256_castsi128_si256( \
232*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)&src_ptr[(i * src_stride) + j])); \
233*77c1e3ccSAndroid Build Coastguard Worker data = _mm256_inserti128_si256( \
234*77c1e3ccSAndroid Build Coastguard Worker data, \
235*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128( \
236*77c1e3ccSAndroid Build Coastguard Worker (__m128i *)&src_ptr[(i * src_stride) + j + src_stride]), \
237*77c1e3ccSAndroid Build Coastguard Worker 1); \
238*77c1e3ccSAndroid Build Coastguard Worker \
239*77c1e3ccSAndroid Build Coastguard Worker __m256i res = convolve_lowbd_x(data, coeffs_h, filt); \
240*77c1e3ccSAndroid Build Coastguard Worker res = \
241*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi16(_mm256_add_epi16(res, round_const_h), round_shift_h); \
242*77c1e3ccSAndroid Build Coastguard Worker _mm256_store_si256((__m256i *)&im_block[i * im_stride], res); \
243*77c1e3ccSAndroid Build Coastguard Worker } \
244*77c1e3ccSAndroid Build Coastguard Worker \
245*77c1e3ccSAndroid Build Coastguard Worker __m256i data_1 = _mm256_castsi128_si256( \
246*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)&src_ptr[(i * src_stride) + j])); \
247*77c1e3ccSAndroid Build Coastguard Worker \
248*77c1e3ccSAndroid Build Coastguard Worker __m256i res = convolve_lowbd_x(data_1, coeffs_h, filt); \
249*77c1e3ccSAndroid Build Coastguard Worker \
250*77c1e3ccSAndroid Build Coastguard Worker res = _mm256_sra_epi16(_mm256_add_epi16(res, round_const_h), round_shift_h); \
251*77c1e3ccSAndroid Build Coastguard Worker \
252*77c1e3ccSAndroid Build Coastguard Worker _mm256_store_si256((__m256i *)&im_block[i * im_stride], res);
253*77c1e3ccSAndroid Build Coastguard Worker
254*77c1e3ccSAndroid Build Coastguard Worker #define CONVOLVE_SR_VERTICAL_FILTER_8TAP \
255*77c1e3ccSAndroid Build Coastguard Worker __m256i src_0 = _mm256_loadu_si256((__m256i *)(im_block + 0 * im_stride)); \
256*77c1e3ccSAndroid Build Coastguard Worker __m256i src_1 = _mm256_loadu_si256((__m256i *)(im_block + 1 * im_stride)); \
257*77c1e3ccSAndroid Build Coastguard Worker __m256i src_2 = _mm256_loadu_si256((__m256i *)(im_block + 2 * im_stride)); \
258*77c1e3ccSAndroid Build Coastguard Worker __m256i src_3 = _mm256_loadu_si256((__m256i *)(im_block + 3 * im_stride)); \
259*77c1e3ccSAndroid Build Coastguard Worker __m256i src_4 = _mm256_loadu_si256((__m256i *)(im_block + 4 * im_stride)); \
260*77c1e3ccSAndroid Build Coastguard Worker __m256i src_5 = _mm256_loadu_si256((__m256i *)(im_block + 5 * im_stride)); \
261*77c1e3ccSAndroid Build Coastguard Worker \
262*77c1e3ccSAndroid Build Coastguard Worker __m256i s[8]; \
263*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_unpacklo_epi16(src_0, src_1); \
264*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_unpacklo_epi16(src_2, src_3); \
265*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_unpacklo_epi16(src_4, src_5); \
266*77c1e3ccSAndroid Build Coastguard Worker \
267*77c1e3ccSAndroid Build Coastguard Worker s[4] = _mm256_unpackhi_epi16(src_0, src_1); \
268*77c1e3ccSAndroid Build Coastguard Worker s[5] = _mm256_unpackhi_epi16(src_2, src_3); \
269*77c1e3ccSAndroid Build Coastguard Worker s[6] = _mm256_unpackhi_epi16(src_4, src_5); \
270*77c1e3ccSAndroid Build Coastguard Worker \
271*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < h; i += 2) { \
272*77c1e3ccSAndroid Build Coastguard Worker const int16_t *data = &im_block[i * im_stride]; \
273*77c1e3ccSAndroid Build Coastguard Worker \
274*77c1e3ccSAndroid Build Coastguard Worker const __m256i s6 = _mm256_loadu_si256((__m256i *)(data + 6 * im_stride)); \
275*77c1e3ccSAndroid Build Coastguard Worker const __m256i s7 = _mm256_loadu_si256((__m256i *)(data + 7 * im_stride)); \
276*77c1e3ccSAndroid Build Coastguard Worker \
277*77c1e3ccSAndroid Build Coastguard Worker s[3] = _mm256_unpacklo_epi16(s6, s7); \
278*77c1e3ccSAndroid Build Coastguard Worker s[7] = _mm256_unpackhi_epi16(s6, s7); \
279*77c1e3ccSAndroid Build Coastguard Worker \
280*77c1e3ccSAndroid Build Coastguard Worker __m256i res_a = convolve(s, coeffs_v); \
281*77c1e3ccSAndroid Build Coastguard Worker __m256i res_b = convolve(s + 4, coeffs_v); \
282*77c1e3ccSAndroid Build Coastguard Worker \
283*77c1e3ccSAndroid Build Coastguard Worker res_a = \
284*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi32(_mm256_add_epi32(res_a, sum_round_v), sum_shift_v); \
285*77c1e3ccSAndroid Build Coastguard Worker res_b = \
286*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi32(_mm256_add_epi32(res_b, sum_round_v), sum_shift_v); \
287*77c1e3ccSAndroid Build Coastguard Worker \
288*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_a_round = _mm256_sra_epi32( \
289*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_a, round_const_v), round_shift_v); \
290*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_b_round = _mm256_sra_epi32( \
291*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_b, round_const_v), round_shift_v); \
292*77c1e3ccSAndroid Build Coastguard Worker \
293*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_16bit = _mm256_packs_epi32(res_a_round, res_b_round); \
294*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_8b = _mm256_packus_epi16(res_16bit, res_16bit); \
295*77c1e3ccSAndroid Build Coastguard Worker \
296*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_castsi256_si128(res_8b); \
297*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_8b, 1); \
298*77c1e3ccSAndroid Build Coastguard Worker \
299*77c1e3ccSAndroid Build Coastguard Worker __m128i *const p_0 = (__m128i *)&dst[i * dst_stride + j]; \
300*77c1e3ccSAndroid Build Coastguard Worker __m128i *const p_1 = (__m128i *)&dst[i * dst_stride + j + dst_stride]; \
301*77c1e3ccSAndroid Build Coastguard Worker if (w - j > 4) { \
302*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64(p_0, res_0); \
303*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64(p_1, res_1); \
304*77c1e3ccSAndroid Build Coastguard Worker } else if (w == 4) { \
305*77c1e3ccSAndroid Build Coastguard Worker xx_storel_32(p_0, res_0); \
306*77c1e3ccSAndroid Build Coastguard Worker xx_storel_32(p_1, res_1); \
307*77c1e3ccSAndroid Build Coastguard Worker } else { \
308*77c1e3ccSAndroid Build Coastguard Worker *(uint16_t *)p_0 = (uint16_t)_mm_cvtsi128_si32(res_0); \
309*77c1e3ccSAndroid Build Coastguard Worker *(uint16_t *)p_1 = (uint16_t)_mm_cvtsi128_si32(res_1); \
310*77c1e3ccSAndroid Build Coastguard Worker } \
311*77c1e3ccSAndroid Build Coastguard Worker \
312*77c1e3ccSAndroid Build Coastguard Worker s[0] = s[1]; \
313*77c1e3ccSAndroid Build Coastguard Worker s[1] = s[2]; \
314*77c1e3ccSAndroid Build Coastguard Worker s[2] = s[3]; \
315*77c1e3ccSAndroid Build Coastguard Worker \
316*77c1e3ccSAndroid Build Coastguard Worker s[4] = s[5]; \
317*77c1e3ccSAndroid Build Coastguard Worker s[5] = s[6]; \
318*77c1e3ccSAndroid Build Coastguard Worker s[6] = s[7]; \
319*77c1e3ccSAndroid Build Coastguard Worker }
320*77c1e3ccSAndroid Build Coastguard Worker
321*77c1e3ccSAndroid Build Coastguard Worker #define CONVOLVE_SR_HORIZONTAL_FILTER_12TAP \
322*77c1e3ccSAndroid Build Coastguard Worker const __m256i v_zero = _mm256_setzero_si256(); \
323*77c1e3ccSAndroid Build Coastguard Worker __m256i s[12]; \
324*77c1e3ccSAndroid Build Coastguard Worker if (w <= 4) { \
325*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < im_h; i += 2) { \
326*77c1e3ccSAndroid Build Coastguard Worker const __m256i data = _mm256_permute2x128_si256( \
327*77c1e3ccSAndroid Build Coastguard Worker _mm256_castsi128_si256( \
328*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)(&src_ptr[i * src_stride + j]))), \
329*77c1e3ccSAndroid Build Coastguard Worker _mm256_castsi128_si256(_mm_loadu_si128( \
330*77c1e3ccSAndroid Build Coastguard Worker (__m128i *)(&src_ptr[i * src_stride + src_stride + j]))), \
331*77c1e3ccSAndroid Build Coastguard Worker 0x20); \
332*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_16lo = _mm256_unpacklo_epi8(data, v_zero); \
333*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_16hi = _mm256_unpackhi_epi8(data, v_zero); \
334*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_lolo = _mm256_unpacklo_epi16(s_16lo, s_16lo); \
335*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_lohi = _mm256_unpackhi_epi16(s_16lo, s_16lo); \
336*77c1e3ccSAndroid Build Coastguard Worker \
337*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_hilo = _mm256_unpacklo_epi16(s_16hi, s_16hi); \
338*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_hihi = _mm256_unpackhi_epi16(s_16hi, s_16hi); \
339*77c1e3ccSAndroid Build Coastguard Worker \
340*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_alignr_epi8(s_lohi, s_lolo, 2); \
341*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_alignr_epi8(s_lohi, s_lolo, 10); \
342*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_alignr_epi8(s_hilo, s_lohi, 2); \
343*77c1e3ccSAndroid Build Coastguard Worker s[3] = _mm256_alignr_epi8(s_hilo, s_lohi, 10); \
344*77c1e3ccSAndroid Build Coastguard Worker s[4] = _mm256_alignr_epi8(s_hihi, s_hilo, 2); \
345*77c1e3ccSAndroid Build Coastguard Worker s[5] = _mm256_alignr_epi8(s_hihi, s_hilo, 10); \
346*77c1e3ccSAndroid Build Coastguard Worker \
347*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_lo = convolve_12taps(s, coeffs_h); \
348*77c1e3ccSAndroid Build Coastguard Worker \
349*77c1e3ccSAndroid Build Coastguard Worker __m256i res_32b_lo = _mm256_sra_epi32( \
350*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_lo, round_const_h12), round_shift_h12); \
351*77c1e3ccSAndroid Build Coastguard Worker __m256i res_16b_lo = _mm256_packs_epi32(res_32b_lo, res_32b_lo); \
352*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_extracti128_si256(res_16b_lo, 0); \
353*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_16b_lo, 1); \
354*77c1e3ccSAndroid Build Coastguard Worker if (w > 2) { \
355*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64((__m128i *)&im_block[i * im_stride], res_0); \
356*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64((__m128i *)&im_block[i * im_stride + im_stride], \
357*77c1e3ccSAndroid Build Coastguard Worker res_1); \
358*77c1e3ccSAndroid Build Coastguard Worker } else { \
359*77c1e3ccSAndroid Build Coastguard Worker uint32_t horiz_2; \
360*77c1e3ccSAndroid Build Coastguard Worker horiz_2 = (uint32_t)_mm_cvtsi128_si32(res_0); \
361*77c1e3ccSAndroid Build Coastguard Worker im_block[i * im_stride] = (uint16_t)horiz_2; \
362*77c1e3ccSAndroid Build Coastguard Worker im_block[i * im_stride + 1] = (uint16_t)(horiz_2 >> 16); \
363*77c1e3ccSAndroid Build Coastguard Worker horiz_2 = (uint32_t)_mm_cvtsi128_si32(res_1); \
364*77c1e3ccSAndroid Build Coastguard Worker im_block[i * im_stride + im_stride] = (uint16_t)horiz_2; \
365*77c1e3ccSAndroid Build Coastguard Worker im_block[i * im_stride + im_stride + 1] = (uint16_t)(horiz_2 >> 16); \
366*77c1e3ccSAndroid Build Coastguard Worker } \
367*77c1e3ccSAndroid Build Coastguard Worker } \
368*77c1e3ccSAndroid Build Coastguard Worker } else { \
369*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < im_h; i++) { \
370*77c1e3ccSAndroid Build Coastguard Worker const __m256i data = _mm256_permute2x128_si256( \
371*77c1e3ccSAndroid Build Coastguard Worker _mm256_castsi128_si256( \
372*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)(&src_ptr[i * src_stride + j]))), \
373*77c1e3ccSAndroid Build Coastguard Worker _mm256_castsi128_si256( \
374*77c1e3ccSAndroid Build Coastguard Worker _mm_loadu_si128((__m128i *)(&src_ptr[i * src_stride + j + 4]))), \
375*77c1e3ccSAndroid Build Coastguard Worker 0x20); \
376*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_16lo = _mm256_unpacklo_epi8(data, v_zero); \
377*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_16hi = _mm256_unpackhi_epi8(data, v_zero); \
378*77c1e3ccSAndroid Build Coastguard Worker \
379*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_lolo = _mm256_unpacklo_epi16(s_16lo, s_16lo); \
380*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_lohi = _mm256_unpackhi_epi16(s_16lo, s_16lo); \
381*77c1e3ccSAndroid Build Coastguard Worker \
382*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_hilo = _mm256_unpacklo_epi16(s_16hi, s_16hi); \
383*77c1e3ccSAndroid Build Coastguard Worker const __m256i s_hihi = _mm256_unpackhi_epi16(s_16hi, s_16hi); \
384*77c1e3ccSAndroid Build Coastguard Worker \
385*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_alignr_epi8(s_lohi, s_lolo, 2); \
386*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_alignr_epi8(s_lohi, s_lolo, 10); \
387*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_alignr_epi8(s_hilo, s_lohi, 2); \
388*77c1e3ccSAndroid Build Coastguard Worker s[3] = _mm256_alignr_epi8(s_hilo, s_lohi, 10); \
389*77c1e3ccSAndroid Build Coastguard Worker s[4] = _mm256_alignr_epi8(s_hihi, s_hilo, 2); \
390*77c1e3ccSAndroid Build Coastguard Worker s[5] = _mm256_alignr_epi8(s_hihi, s_hilo, 10); \
391*77c1e3ccSAndroid Build Coastguard Worker \
392*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_lo = convolve_12taps(s, coeffs_h); \
393*77c1e3ccSAndroid Build Coastguard Worker \
394*77c1e3ccSAndroid Build Coastguard Worker __m256i res_32b_lo = _mm256_sra_epi32( \
395*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_lo, round_const_h12), round_shift_h12); \
396*77c1e3ccSAndroid Build Coastguard Worker \
397*77c1e3ccSAndroid Build Coastguard Worker __m256i res_16b_lo = _mm256_packs_epi32(res_32b_lo, res_32b_lo); \
398*77c1e3ccSAndroid Build Coastguard Worker _mm_store_si128((__m128i *)&im_block[i * im_stride], \
399*77c1e3ccSAndroid Build Coastguard Worker _mm256_extracti128_si256( \
400*77c1e3ccSAndroid Build Coastguard Worker _mm256_permute4x64_epi64(res_16b_lo, 0x88), 0)); \
401*77c1e3ccSAndroid Build Coastguard Worker } \
402*77c1e3ccSAndroid Build Coastguard Worker }
403*77c1e3ccSAndroid Build Coastguard Worker
404*77c1e3ccSAndroid Build Coastguard Worker #define CONVOLVE_SR_VERTICAL_FILTER_12TAP \
405*77c1e3ccSAndroid Build Coastguard Worker __m256i src_0 = _mm256_loadu_si256((__m256i *)(im_block + 0 * im_stride)); \
406*77c1e3ccSAndroid Build Coastguard Worker __m256i src_1 = _mm256_loadu_si256((__m256i *)(im_block + 1 * im_stride)); \
407*77c1e3ccSAndroid Build Coastguard Worker __m256i src_2 = _mm256_loadu_si256((__m256i *)(im_block + 2 * im_stride)); \
408*77c1e3ccSAndroid Build Coastguard Worker __m256i src_3 = _mm256_loadu_si256((__m256i *)(im_block + 3 * im_stride)); \
409*77c1e3ccSAndroid Build Coastguard Worker __m256i src_4 = _mm256_loadu_si256((__m256i *)(im_block + 4 * im_stride)); \
410*77c1e3ccSAndroid Build Coastguard Worker __m256i src_5 = _mm256_loadu_si256((__m256i *)(im_block + 5 * im_stride)); \
411*77c1e3ccSAndroid Build Coastguard Worker __m256i src_6 = _mm256_loadu_si256((__m256i *)(im_block + 6 * im_stride)); \
412*77c1e3ccSAndroid Build Coastguard Worker __m256i src_7 = _mm256_loadu_si256((__m256i *)(im_block + 7 * im_stride)); \
413*77c1e3ccSAndroid Build Coastguard Worker __m256i src_8 = _mm256_loadu_si256((__m256i *)(im_block + 8 * im_stride)); \
414*77c1e3ccSAndroid Build Coastguard Worker __m256i src_9 = _mm256_loadu_si256((__m256i *)(im_block + 9 * im_stride)); \
415*77c1e3ccSAndroid Build Coastguard Worker \
416*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_unpacklo_epi16(src_0, src_1); \
417*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_unpacklo_epi16(src_2, src_3); \
418*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_unpacklo_epi16(src_4, src_5); \
419*77c1e3ccSAndroid Build Coastguard Worker s[3] = _mm256_unpacklo_epi16(src_6, src_7); \
420*77c1e3ccSAndroid Build Coastguard Worker s[4] = _mm256_unpacklo_epi16(src_8, src_9); \
421*77c1e3ccSAndroid Build Coastguard Worker \
422*77c1e3ccSAndroid Build Coastguard Worker s[6] = _mm256_unpackhi_epi16(src_0, src_1); \
423*77c1e3ccSAndroid Build Coastguard Worker s[7] = _mm256_unpackhi_epi16(src_2, src_3); \
424*77c1e3ccSAndroid Build Coastguard Worker s[8] = _mm256_unpackhi_epi16(src_4, src_5); \
425*77c1e3ccSAndroid Build Coastguard Worker s[9] = _mm256_unpackhi_epi16(src_6, src_7); \
426*77c1e3ccSAndroid Build Coastguard Worker s[10] = _mm256_unpackhi_epi16(src_8, src_9); \
427*77c1e3ccSAndroid Build Coastguard Worker \
428*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < h; i += 2) { \
429*77c1e3ccSAndroid Build Coastguard Worker const int16_t *data = &im_block[i * im_stride]; \
430*77c1e3ccSAndroid Build Coastguard Worker \
431*77c1e3ccSAndroid Build Coastguard Worker const __m256i s6 = _mm256_loadu_si256((__m256i *)(data + 10 * im_stride)); \
432*77c1e3ccSAndroid Build Coastguard Worker const __m256i s7 = _mm256_loadu_si256((__m256i *)(data + 11 * im_stride)); \
433*77c1e3ccSAndroid Build Coastguard Worker \
434*77c1e3ccSAndroid Build Coastguard Worker s[5] = _mm256_unpacklo_epi16(s6, s7); \
435*77c1e3ccSAndroid Build Coastguard Worker s[11] = _mm256_unpackhi_epi16(s6, s7); \
436*77c1e3ccSAndroid Build Coastguard Worker \
437*77c1e3ccSAndroid Build Coastguard Worker __m256i res_a = convolve_12taps(s, coeffs_v); \
438*77c1e3ccSAndroid Build Coastguard Worker __m256i res_b = convolve_12taps(s + 6, coeffs_v); \
439*77c1e3ccSAndroid Build Coastguard Worker \
440*77c1e3ccSAndroid Build Coastguard Worker res_a = \
441*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi32(_mm256_add_epi32(res_a, sum_round_v), sum_shift_v); \
442*77c1e3ccSAndroid Build Coastguard Worker res_b = \
443*77c1e3ccSAndroid Build Coastguard Worker _mm256_sra_epi32(_mm256_add_epi32(res_b, sum_round_v), sum_shift_v); \
444*77c1e3ccSAndroid Build Coastguard Worker \
445*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_a_round = _mm256_sra_epi32( \
446*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_a, round_const_v), round_shift_v); \
447*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_b_round = _mm256_sra_epi32( \
448*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_b, round_const_v), round_shift_v); \
449*77c1e3ccSAndroid Build Coastguard Worker \
450*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_16bit = _mm256_packs_epi32(res_a_round, res_b_round); \
451*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_8b = _mm256_packus_epi16(res_16bit, res_16bit); \
452*77c1e3ccSAndroid Build Coastguard Worker \
453*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_castsi256_si128(res_8b); \
454*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_8b, 1); \
455*77c1e3ccSAndroid Build Coastguard Worker \
456*77c1e3ccSAndroid Build Coastguard Worker __m128i *const p_0 = (__m128i *)&dst[i * dst_stride + j]; \
457*77c1e3ccSAndroid Build Coastguard Worker __m128i *const p_1 = (__m128i *)&dst[i * dst_stride + j + dst_stride]; \
458*77c1e3ccSAndroid Build Coastguard Worker if (w - j > 4) { \
459*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64(p_0, res_0); \
460*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64(p_1, res_1); \
461*77c1e3ccSAndroid Build Coastguard Worker } else if (w == 4) { \
462*77c1e3ccSAndroid Build Coastguard Worker xx_storel_32(p_0, res_0); \
463*77c1e3ccSAndroid Build Coastguard Worker xx_storel_32(p_1, res_1); \
464*77c1e3ccSAndroid Build Coastguard Worker } else { \
465*77c1e3ccSAndroid Build Coastguard Worker *(uint16_t *)p_0 = (uint16_t)_mm_cvtsi128_si32(res_0); \
466*77c1e3ccSAndroid Build Coastguard Worker *(uint16_t *)p_1 = (uint16_t)_mm_cvtsi128_si32(res_1); \
467*77c1e3ccSAndroid Build Coastguard Worker } \
468*77c1e3ccSAndroid Build Coastguard Worker \
469*77c1e3ccSAndroid Build Coastguard Worker s[0] = s[1]; \
470*77c1e3ccSAndroid Build Coastguard Worker s[1] = s[2]; \
471*77c1e3ccSAndroid Build Coastguard Worker s[2] = s[3]; \
472*77c1e3ccSAndroid Build Coastguard Worker s[3] = s[4]; \
473*77c1e3ccSAndroid Build Coastguard Worker s[4] = s[5]; \
474*77c1e3ccSAndroid Build Coastguard Worker \
475*77c1e3ccSAndroid Build Coastguard Worker s[6] = s[7]; \
476*77c1e3ccSAndroid Build Coastguard Worker s[7] = s[8]; \
477*77c1e3ccSAndroid Build Coastguard Worker s[8] = s[9]; \
478*77c1e3ccSAndroid Build Coastguard Worker s[9] = s[10]; \
479*77c1e3ccSAndroid Build Coastguard Worker s[10] = s[11]; \
480*77c1e3ccSAndroid Build Coastguard Worker }
481*77c1e3ccSAndroid Build Coastguard Worker
482*77c1e3ccSAndroid Build Coastguard Worker #define DIST_WTD_CONVOLVE_HORIZONTAL_FILTER_8TAP \
483*77c1e3ccSAndroid Build Coastguard Worker do { \
484*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < im_h; i += 2) { \
485*77c1e3ccSAndroid Build Coastguard Worker __m256i data = \
486*77c1e3ccSAndroid Build Coastguard Worker _mm256_castsi128_si256(_mm_loadu_si128((__m128i *)src_h)); \
487*77c1e3ccSAndroid Build Coastguard Worker if (i + 1 < im_h) \
488*77c1e3ccSAndroid Build Coastguard Worker data = _mm256_inserti128_si256( \
489*77c1e3ccSAndroid Build Coastguard Worker data, _mm_loadu_si128((__m128i *)(src_h + src_stride)), 1); \
490*77c1e3ccSAndroid Build Coastguard Worker src_h += (src_stride << 1); \
491*77c1e3ccSAndroid Build Coastguard Worker __m256i res = convolve_lowbd_x(data, coeffs_x, filt); \
492*77c1e3ccSAndroid Build Coastguard Worker \
493*77c1e3ccSAndroid Build Coastguard Worker res = _mm256_sra_epi16(_mm256_add_epi16(res, round_const_h), \
494*77c1e3ccSAndroid Build Coastguard Worker round_shift_h); \
495*77c1e3ccSAndroid Build Coastguard Worker \
496*77c1e3ccSAndroid Build Coastguard Worker _mm256_store_si256((__m256i *)&im_block[i * im_stride], res); \
497*77c1e3ccSAndroid Build Coastguard Worker } \
498*77c1e3ccSAndroid Build Coastguard Worker } while (0)
499*77c1e3ccSAndroid Build Coastguard Worker
500*77c1e3ccSAndroid Build Coastguard Worker #define DIST_WTD_CONVOLVE_VERTICAL_FILTER_8TAP \
501*77c1e3ccSAndroid Build Coastguard Worker do { \
502*77c1e3ccSAndroid Build Coastguard Worker __m256i s[8]; \
503*77c1e3ccSAndroid Build Coastguard Worker __m256i s0 = _mm256_loadu_si256((__m256i *)(im_block + 0 * im_stride)); \
504*77c1e3ccSAndroid Build Coastguard Worker __m256i s1 = _mm256_loadu_si256((__m256i *)(im_block + 1 * im_stride)); \
505*77c1e3ccSAndroid Build Coastguard Worker __m256i s2 = _mm256_loadu_si256((__m256i *)(im_block + 2 * im_stride)); \
506*77c1e3ccSAndroid Build Coastguard Worker __m256i s3 = _mm256_loadu_si256((__m256i *)(im_block + 3 * im_stride)); \
507*77c1e3ccSAndroid Build Coastguard Worker __m256i s4 = _mm256_loadu_si256((__m256i *)(im_block + 4 * im_stride)); \
508*77c1e3ccSAndroid Build Coastguard Worker __m256i s5 = _mm256_loadu_si256((__m256i *)(im_block + 5 * im_stride)); \
509*77c1e3ccSAndroid Build Coastguard Worker \
510*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_unpacklo_epi16(s0, s1); \
511*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_unpacklo_epi16(s2, s3); \
512*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_unpacklo_epi16(s4, s5); \
513*77c1e3ccSAndroid Build Coastguard Worker \
514*77c1e3ccSAndroid Build Coastguard Worker s[4] = _mm256_unpackhi_epi16(s0, s1); \
515*77c1e3ccSAndroid Build Coastguard Worker s[5] = _mm256_unpackhi_epi16(s2, s3); \
516*77c1e3ccSAndroid Build Coastguard Worker s[6] = _mm256_unpackhi_epi16(s4, s5); \
517*77c1e3ccSAndroid Build Coastguard Worker \
518*77c1e3ccSAndroid Build Coastguard Worker for (i = 0; i < h; i += 2) { \
519*77c1e3ccSAndroid Build Coastguard Worker const int16_t *data = &im_block[i * im_stride]; \
520*77c1e3ccSAndroid Build Coastguard Worker \
521*77c1e3ccSAndroid Build Coastguard Worker const __m256i s6 = \
522*77c1e3ccSAndroid Build Coastguard Worker _mm256_loadu_si256((__m256i *)(data + 6 * im_stride)); \
523*77c1e3ccSAndroid Build Coastguard Worker const __m256i s7 = \
524*77c1e3ccSAndroid Build Coastguard Worker _mm256_loadu_si256((__m256i *)(data + 7 * im_stride)); \
525*77c1e3ccSAndroid Build Coastguard Worker \
526*77c1e3ccSAndroid Build Coastguard Worker s[3] = _mm256_unpacklo_epi16(s6, s7); \
527*77c1e3ccSAndroid Build Coastguard Worker s[7] = _mm256_unpackhi_epi16(s6, s7); \
528*77c1e3ccSAndroid Build Coastguard Worker \
529*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_a = convolve(s, coeffs_y); \
530*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_a_round = _mm256_sra_epi32( \
531*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_a, round_const_v), round_shift_v); \
532*77c1e3ccSAndroid Build Coastguard Worker \
533*77c1e3ccSAndroid Build Coastguard Worker if (w - j > 4) { \
534*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_b = convolve(s + 4, coeffs_y); \
535*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_b_round = _mm256_sra_epi32( \
536*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_b, round_const_v), round_shift_v); \
537*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_16b = _mm256_packs_epi32(res_a_round, res_b_round); \
538*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_unsigned = _mm256_add_epi16(res_16b, offset_const); \
539*77c1e3ccSAndroid Build Coastguard Worker \
540*77c1e3ccSAndroid Build Coastguard Worker if (do_average) { \
541*77c1e3ccSAndroid Build Coastguard Worker const __m256i data_ref_0 = \
542*77c1e3ccSAndroid Build Coastguard Worker load_line2_avx2(&dst[i * dst_stride + j], \
543*77c1e3ccSAndroid Build Coastguard Worker &dst[i * dst_stride + j + dst_stride]); \
544*77c1e3ccSAndroid Build Coastguard Worker const __m256i comp_avg_res = comp_avg(&data_ref_0, &res_unsigned, \
545*77c1e3ccSAndroid Build Coastguard Worker &wt, use_dist_wtd_comp_avg); \
546*77c1e3ccSAndroid Build Coastguard Worker \
547*77c1e3ccSAndroid Build Coastguard Worker const __m256i round_result = convolve_rounding( \
548*77c1e3ccSAndroid Build Coastguard Worker &comp_avg_res, &offset_const, &rounding_const, rounding_shift); \
549*77c1e3ccSAndroid Build Coastguard Worker \
550*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_8 = \
551*77c1e3ccSAndroid Build Coastguard Worker _mm256_packus_epi16(round_result, round_result); \
552*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_castsi256_si128(res_8); \
553*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_8, 1); \
554*77c1e3ccSAndroid Build Coastguard Worker \
555*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64((__m128i *)(&dst0[i * dst_stride0 + j]), res_0); \
556*77c1e3ccSAndroid Build Coastguard Worker _mm_storel_epi64( \
557*77c1e3ccSAndroid Build Coastguard Worker (__m128i *)((&dst0[i * dst_stride0 + j + dst_stride0])), res_1); \
558*77c1e3ccSAndroid Build Coastguard Worker } else { \
559*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_castsi256_si128(res_unsigned); \
560*77c1e3ccSAndroid Build Coastguard Worker _mm_store_si128((__m128i *)(&dst[i * dst_stride + j]), res_0); \
561*77c1e3ccSAndroid Build Coastguard Worker \
562*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_unsigned, 1); \
563*77c1e3ccSAndroid Build Coastguard Worker _mm_store_si128((__m128i *)(&dst[i * dst_stride + j + dst_stride]), \
564*77c1e3ccSAndroid Build Coastguard Worker res_1); \
565*77c1e3ccSAndroid Build Coastguard Worker } \
566*77c1e3ccSAndroid Build Coastguard Worker } else { \
567*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_16b = _mm256_packs_epi32(res_a_round, res_a_round); \
568*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_unsigned = _mm256_add_epi16(res_16b, offset_const); \
569*77c1e3ccSAndroid Build Coastguard Worker \
570*77c1e3ccSAndroid Build Coastguard Worker if (do_average) { \
571*77c1e3ccSAndroid Build Coastguard Worker const __m256i data_ref_0 = \
572*77c1e3ccSAndroid Build Coastguard Worker load_line2_avx2(&dst[i * dst_stride + j], \
573*77c1e3ccSAndroid Build Coastguard Worker &dst[i * dst_stride + j + dst_stride]); \
574*77c1e3ccSAndroid Build Coastguard Worker \
575*77c1e3ccSAndroid Build Coastguard Worker const __m256i comp_avg_res = comp_avg(&data_ref_0, &res_unsigned, \
576*77c1e3ccSAndroid Build Coastguard Worker &wt, use_dist_wtd_comp_avg); \
577*77c1e3ccSAndroid Build Coastguard Worker \
578*77c1e3ccSAndroid Build Coastguard Worker const __m256i round_result = convolve_rounding( \
579*77c1e3ccSAndroid Build Coastguard Worker &comp_avg_res, &offset_const, &rounding_const, rounding_shift); \
580*77c1e3ccSAndroid Build Coastguard Worker \
581*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_8 = \
582*77c1e3ccSAndroid Build Coastguard Worker _mm256_packus_epi16(round_result, round_result); \
583*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_castsi256_si128(res_8); \
584*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_8, 1); \
585*77c1e3ccSAndroid Build Coastguard Worker \
586*77c1e3ccSAndroid Build Coastguard Worker *(int *)(&dst0[i * dst_stride0 + j]) = _mm_cvtsi128_si32(res_0); \
587*77c1e3ccSAndroid Build Coastguard Worker *(int *)(&dst0[i * dst_stride0 + j + dst_stride0]) = \
588*77c1e3ccSAndroid Build Coastguard Worker _mm_cvtsi128_si32(res_1); \
589*77c1e3ccSAndroid Build Coastguard Worker \
590*77c1e3ccSAndroid Build Coastguard Worker } else { \
591*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_0 = _mm256_castsi256_si128(res_unsigned); \
592*77c1e3ccSAndroid Build Coastguard Worker _mm_store_si128((__m128i *)(&dst[i * dst_stride + j]), res_0); \
593*77c1e3ccSAndroid Build Coastguard Worker \
594*77c1e3ccSAndroid Build Coastguard Worker const __m128i res_1 = _mm256_extracti128_si256(res_unsigned, 1); \
595*77c1e3ccSAndroid Build Coastguard Worker _mm_store_si128((__m128i *)(&dst[i * dst_stride + j + dst_stride]), \
596*77c1e3ccSAndroid Build Coastguard Worker res_1); \
597*77c1e3ccSAndroid Build Coastguard Worker } \
598*77c1e3ccSAndroid Build Coastguard Worker } \
599*77c1e3ccSAndroid Build Coastguard Worker \
600*77c1e3ccSAndroid Build Coastguard Worker s[0] = s[1]; \
601*77c1e3ccSAndroid Build Coastguard Worker s[1] = s[2]; \
602*77c1e3ccSAndroid Build Coastguard Worker s[2] = s[3]; \
603*77c1e3ccSAndroid Build Coastguard Worker \
604*77c1e3ccSAndroid Build Coastguard Worker s[4] = s[5]; \
605*77c1e3ccSAndroid Build Coastguard Worker s[5] = s[6]; \
606*77c1e3ccSAndroid Build Coastguard Worker s[6] = s[7]; \
607*77c1e3ccSAndroid Build Coastguard Worker } \
608*77c1e3ccSAndroid Build Coastguard Worker } while (0)
609*77c1e3ccSAndroid Build Coastguard Worker
prepare_coeffs_lowbd(const InterpFilterParams * const filter_params,const int subpel_q4,__m256i * const coeffs)610*77c1e3ccSAndroid Build Coastguard Worker static inline void prepare_coeffs_lowbd(
611*77c1e3ccSAndroid Build Coastguard Worker const InterpFilterParams *const filter_params, const int subpel_q4,
612*77c1e3ccSAndroid Build Coastguard Worker __m256i *const coeffs /* [4] */) {
613*77c1e3ccSAndroid Build Coastguard Worker const int16_t *const filter = av1_get_interp_filter_subpel_kernel(
614*77c1e3ccSAndroid Build Coastguard Worker filter_params, subpel_q4 & SUBPEL_MASK);
615*77c1e3ccSAndroid Build Coastguard Worker const __m128i coeffs_8 = _mm_loadu_si128((__m128i *)filter);
616*77c1e3ccSAndroid Build Coastguard Worker const __m256i filter_coeffs = _mm256_broadcastsi128_si256(coeffs_8);
617*77c1e3ccSAndroid Build Coastguard Worker
618*77c1e3ccSAndroid Build Coastguard Worker // right shift all filter co-efficients by 1 to reduce the bits required.
619*77c1e3ccSAndroid Build Coastguard Worker // This extra right shift will be taken care of at the end while rounding
620*77c1e3ccSAndroid Build Coastguard Worker // the result.
621*77c1e3ccSAndroid Build Coastguard Worker // Since all filter co-efficients are even, this change will not affect the
622*77c1e3ccSAndroid Build Coastguard Worker // end result
623*77c1e3ccSAndroid Build Coastguard Worker assert(_mm_test_all_zeros(_mm_and_si128(coeffs_8, _mm_set1_epi16(1)),
624*77c1e3ccSAndroid Build Coastguard Worker _mm_set1_epi16((short)0xffff)));
625*77c1e3ccSAndroid Build Coastguard Worker
626*77c1e3ccSAndroid Build Coastguard Worker const __m256i coeffs_1 = _mm256_srai_epi16(filter_coeffs, 1);
627*77c1e3ccSAndroid Build Coastguard Worker
628*77c1e3ccSAndroid Build Coastguard Worker // coeffs 0 1 0 1 0 1 0 1
629*77c1e3ccSAndroid Build Coastguard Worker coeffs[0] = _mm256_shuffle_epi8(coeffs_1, _mm256_set1_epi16(0x0200u));
630*77c1e3ccSAndroid Build Coastguard Worker // coeffs 2 3 2 3 2 3 2 3
631*77c1e3ccSAndroid Build Coastguard Worker coeffs[1] = _mm256_shuffle_epi8(coeffs_1, _mm256_set1_epi16(0x0604u));
632*77c1e3ccSAndroid Build Coastguard Worker // coeffs 4 5 4 5 4 5 4 5
633*77c1e3ccSAndroid Build Coastguard Worker coeffs[2] = _mm256_shuffle_epi8(coeffs_1, _mm256_set1_epi16(0x0a08u));
634*77c1e3ccSAndroid Build Coastguard Worker // coeffs 6 7 6 7 6 7 6 7
635*77c1e3ccSAndroid Build Coastguard Worker coeffs[3] = _mm256_shuffle_epi8(coeffs_1, _mm256_set1_epi16(0x0e0cu));
636*77c1e3ccSAndroid Build Coastguard Worker }
637*77c1e3ccSAndroid Build Coastguard Worker
prepare_coeffs_6t_lowbd(const InterpFilterParams * const filter_params,const int subpel_q4,__m256i * const coeffs)638*77c1e3ccSAndroid Build Coastguard Worker static inline void prepare_coeffs_6t_lowbd(
639*77c1e3ccSAndroid Build Coastguard Worker const InterpFilterParams *const filter_params, const int subpel_q4,
640*77c1e3ccSAndroid Build Coastguard Worker __m256i *const coeffs /* [4] */) {
641*77c1e3ccSAndroid Build Coastguard Worker const int16_t *const filter = av1_get_interp_filter_subpel_kernel(
642*77c1e3ccSAndroid Build Coastguard Worker filter_params, subpel_q4 & SUBPEL_MASK);
643*77c1e3ccSAndroid Build Coastguard Worker const __m128i coeffs_8 = _mm_loadu_si128((__m128i *)filter);
644*77c1e3ccSAndroid Build Coastguard Worker const __m256i filter_coeffs = _mm256_broadcastsi128_si256(coeffs_8);
645*77c1e3ccSAndroid Build Coastguard Worker
646*77c1e3ccSAndroid Build Coastguard Worker // right shift all filter co-efficients by 1 to reduce the bits required.
647*77c1e3ccSAndroid Build Coastguard Worker // This extra right shift will be taken care of at the end while rounding
648*77c1e3ccSAndroid Build Coastguard Worker // the result.
649*77c1e3ccSAndroid Build Coastguard Worker // Since all filter co-efficients are even, this change will not affect the
650*77c1e3ccSAndroid Build Coastguard Worker // end result
651*77c1e3ccSAndroid Build Coastguard Worker assert(_mm_test_all_zeros(_mm_and_si128(coeffs_8, _mm_set1_epi16(1)),
652*77c1e3ccSAndroid Build Coastguard Worker _mm_set1_epi16((int16_t)0xffff)));
653*77c1e3ccSAndroid Build Coastguard Worker
654*77c1e3ccSAndroid Build Coastguard Worker const __m256i coeffs_1 = _mm256_srai_epi16(filter_coeffs, 1);
655*77c1e3ccSAndroid Build Coastguard Worker
656*77c1e3ccSAndroid Build Coastguard Worker // coeffs 1 2 1 2 1 2 1 2
657*77c1e3ccSAndroid Build Coastguard Worker coeffs[0] = _mm256_shuffle_epi8(coeffs_1, _mm256_set1_epi16(0x0402u));
658*77c1e3ccSAndroid Build Coastguard Worker // coeffs 3 4 3 4 3 4 3 4
659*77c1e3ccSAndroid Build Coastguard Worker coeffs[1] = _mm256_shuffle_epi8(coeffs_1, _mm256_set1_epi16(0x0806u));
660*77c1e3ccSAndroid Build Coastguard Worker // coeffs 5 6 5 6 5 6 5 6
661*77c1e3ccSAndroid Build Coastguard Worker coeffs[2] = _mm256_shuffle_epi8(coeffs_1, _mm256_set1_epi16(0x0c0au));
662*77c1e3ccSAndroid Build Coastguard Worker }
663*77c1e3ccSAndroid Build Coastguard Worker
prepare_coeffs_6t(const InterpFilterParams * const filter_params,const int subpel_q4,__m256i * const coeffs)664*77c1e3ccSAndroid Build Coastguard Worker static inline void prepare_coeffs_6t(
665*77c1e3ccSAndroid Build Coastguard Worker const InterpFilterParams *const filter_params, const int subpel_q4,
666*77c1e3ccSAndroid Build Coastguard Worker __m256i *const coeffs /* [4] */) {
667*77c1e3ccSAndroid Build Coastguard Worker const int16_t *filter = av1_get_interp_filter_subpel_kernel(
668*77c1e3ccSAndroid Build Coastguard Worker filter_params, subpel_q4 & SUBPEL_MASK);
669*77c1e3ccSAndroid Build Coastguard Worker
670*77c1e3ccSAndroid Build Coastguard Worker const __m128i coeff_8 = _mm_loadu_si128((__m128i *)(filter + 1));
671*77c1e3ccSAndroid Build Coastguard Worker const __m256i coeff = _mm256_broadcastsi128_si256(coeff_8);
672*77c1e3ccSAndroid Build Coastguard Worker
673*77c1e3ccSAndroid Build Coastguard Worker // coeffs 1 2 1 2 1 2 1 2
674*77c1e3ccSAndroid Build Coastguard Worker coeffs[0] = _mm256_shuffle_epi32(coeff, 0x00);
675*77c1e3ccSAndroid Build Coastguard Worker // coeffs 3 4 3 4 3 4 3 4
676*77c1e3ccSAndroid Build Coastguard Worker coeffs[1] = _mm256_shuffle_epi32(coeff, 0x55);
677*77c1e3ccSAndroid Build Coastguard Worker // coeffs 5 6 5 6 5 6 5 6
678*77c1e3ccSAndroid Build Coastguard Worker coeffs[2] = _mm256_shuffle_epi32(coeff, 0xaa);
679*77c1e3ccSAndroid Build Coastguard Worker }
680*77c1e3ccSAndroid Build Coastguard Worker
prepare_coeffs(const InterpFilterParams * const filter_params,const int subpel_q4,__m256i * const coeffs)681*77c1e3ccSAndroid Build Coastguard Worker static inline void prepare_coeffs(const InterpFilterParams *const filter_params,
682*77c1e3ccSAndroid Build Coastguard Worker const int subpel_q4,
683*77c1e3ccSAndroid Build Coastguard Worker __m256i *const coeffs /* [4] */) {
684*77c1e3ccSAndroid Build Coastguard Worker const int16_t *filter = av1_get_interp_filter_subpel_kernel(
685*77c1e3ccSAndroid Build Coastguard Worker filter_params, subpel_q4 & SUBPEL_MASK);
686*77c1e3ccSAndroid Build Coastguard Worker
687*77c1e3ccSAndroid Build Coastguard Worker const __m128i coeff_8 = _mm_loadu_si128((__m128i *)filter);
688*77c1e3ccSAndroid Build Coastguard Worker const __m256i coeff = _mm256_broadcastsi128_si256(coeff_8);
689*77c1e3ccSAndroid Build Coastguard Worker
690*77c1e3ccSAndroid Build Coastguard Worker // coeffs 0 1 0 1 0 1 0 1
691*77c1e3ccSAndroid Build Coastguard Worker coeffs[0] = _mm256_shuffle_epi32(coeff, 0x00);
692*77c1e3ccSAndroid Build Coastguard Worker // coeffs 2 3 2 3 2 3 2 3
693*77c1e3ccSAndroid Build Coastguard Worker coeffs[1] = _mm256_shuffle_epi32(coeff, 0x55);
694*77c1e3ccSAndroid Build Coastguard Worker // coeffs 4 5 4 5 4 5 4 5
695*77c1e3ccSAndroid Build Coastguard Worker coeffs[2] = _mm256_shuffle_epi32(coeff, 0xaa);
696*77c1e3ccSAndroid Build Coastguard Worker // coeffs 6 7 6 7 6 7 6 7
697*77c1e3ccSAndroid Build Coastguard Worker coeffs[3] = _mm256_shuffle_epi32(coeff, 0xff);
698*77c1e3ccSAndroid Build Coastguard Worker }
699*77c1e3ccSAndroid Build Coastguard Worker
prepare_coeffs_12taps(const InterpFilterParams * const filter_params,const int subpel_q4,__m256i * const coeffs)700*77c1e3ccSAndroid Build Coastguard Worker static inline void prepare_coeffs_12taps(
701*77c1e3ccSAndroid Build Coastguard Worker const InterpFilterParams *const filter_params, const int subpel_q4,
702*77c1e3ccSAndroid Build Coastguard Worker __m256i *const coeffs /* [4] */) {
703*77c1e3ccSAndroid Build Coastguard Worker const int16_t *filter = av1_get_interp_filter_subpel_kernel(
704*77c1e3ccSAndroid Build Coastguard Worker filter_params, subpel_q4 & SUBPEL_MASK);
705*77c1e3ccSAndroid Build Coastguard Worker
706*77c1e3ccSAndroid Build Coastguard Worker __m128i coeff_8 = _mm_loadu_si128((__m128i *)filter);
707*77c1e3ccSAndroid Build Coastguard Worker __m256i coeff = _mm256_broadcastsi128_si256(coeff_8);
708*77c1e3ccSAndroid Build Coastguard Worker
709*77c1e3ccSAndroid Build Coastguard Worker // coeffs 0 1 0 1 0 1 0 1
710*77c1e3ccSAndroid Build Coastguard Worker coeffs[0] = _mm256_shuffle_epi32(coeff, 0x00);
711*77c1e3ccSAndroid Build Coastguard Worker // coeffs 2 3 2 3 2 3 2 3
712*77c1e3ccSAndroid Build Coastguard Worker coeffs[1] = _mm256_shuffle_epi32(coeff, 0x55);
713*77c1e3ccSAndroid Build Coastguard Worker // coeffs 4 5 4 5 4 5 4 5
714*77c1e3ccSAndroid Build Coastguard Worker coeffs[2] = _mm256_shuffle_epi32(coeff, 0xaa);
715*77c1e3ccSAndroid Build Coastguard Worker // coeffs 6 7 6 7 6 7 6 7
716*77c1e3ccSAndroid Build Coastguard Worker coeffs[3] = _mm256_shuffle_epi32(coeff, 0xff);
717*77c1e3ccSAndroid Build Coastguard Worker // coeffs 8 9 10 11 0 0 0 0
718*77c1e3ccSAndroid Build Coastguard Worker coeff_8 = _mm_loadl_epi64((__m128i *)(filter + 8));
719*77c1e3ccSAndroid Build Coastguard Worker coeff = _mm256_broadcastq_epi64(coeff_8);
720*77c1e3ccSAndroid Build Coastguard Worker coeffs[4] = _mm256_shuffle_epi32(coeff, 0x00); // coeffs 8 9 8 9 8 9 8 9
721*77c1e3ccSAndroid Build Coastguard Worker coeffs[5] = _mm256_shuffle_epi32(coeff, 0x55); // coeffs 10 11 10 11.. 10 11
722*77c1e3ccSAndroid Build Coastguard Worker }
723*77c1e3ccSAndroid Build Coastguard Worker
convolve_lowbd(const __m256i * const s,const __m256i * const coeffs)724*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_lowbd(const __m256i *const s,
725*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs) {
726*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_01 = _mm256_maddubs_epi16(s[0], coeffs[0]);
727*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_23 = _mm256_maddubs_epi16(s[1], coeffs[1]);
728*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_45 = _mm256_maddubs_epi16(s[2], coeffs[2]);
729*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_67 = _mm256_maddubs_epi16(s[3], coeffs[3]);
730*77c1e3ccSAndroid Build Coastguard Worker
731*77c1e3ccSAndroid Build Coastguard Worker // order: 0 1 2 3 4 5 6 7 8 9 10 11 12 13 14 15
732*77c1e3ccSAndroid Build Coastguard Worker const __m256i res = _mm256_add_epi16(_mm256_add_epi16(res_01, res_45),
733*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi16(res_23, res_67));
734*77c1e3ccSAndroid Build Coastguard Worker
735*77c1e3ccSAndroid Build Coastguard Worker return res;
736*77c1e3ccSAndroid Build Coastguard Worker }
737*77c1e3ccSAndroid Build Coastguard Worker
convolve_lowbd_6tap(const __m256i * const s,const __m256i * const coeffs)738*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_lowbd_6tap(const __m256i *const s,
739*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs) {
740*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_01 = _mm256_maddubs_epi16(s[0], coeffs[0]);
741*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_23 = _mm256_maddubs_epi16(s[1], coeffs[1]);
742*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_45 = _mm256_maddubs_epi16(s[2], coeffs[2]);
743*77c1e3ccSAndroid Build Coastguard Worker
744*77c1e3ccSAndroid Build Coastguard Worker // order: 0 1 2 3 4 5 6 7 8 9 10 11 12 13 14 15
745*77c1e3ccSAndroid Build Coastguard Worker const __m256i res =
746*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi16(_mm256_add_epi16(res_01, res_45), res_23);
747*77c1e3ccSAndroid Build Coastguard Worker
748*77c1e3ccSAndroid Build Coastguard Worker return res;
749*77c1e3ccSAndroid Build Coastguard Worker }
750*77c1e3ccSAndroid Build Coastguard Worker
convolve_lowbd_4tap(const __m256i * const s,const __m256i * const coeffs)751*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_lowbd_4tap(const __m256i *const s,
752*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs) {
753*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_23 = _mm256_maddubs_epi16(s[0], coeffs[0]);
754*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_45 = _mm256_maddubs_epi16(s[1], coeffs[1]);
755*77c1e3ccSAndroid Build Coastguard Worker
756*77c1e3ccSAndroid Build Coastguard Worker // order: 0 1 2 3 4 5 6 7 8 9 10 11 12 13 14 15
757*77c1e3ccSAndroid Build Coastguard Worker const __m256i res = _mm256_add_epi16(res_45, res_23);
758*77c1e3ccSAndroid Build Coastguard Worker
759*77c1e3ccSAndroid Build Coastguard Worker return res;
760*77c1e3ccSAndroid Build Coastguard Worker }
761*77c1e3ccSAndroid Build Coastguard Worker
convolve_6tap(const __m256i * const s,const __m256i * const coeffs)762*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_6tap(const __m256i *const s,
763*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs) {
764*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_0 = _mm256_madd_epi16(s[0], coeffs[0]);
765*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_1 = _mm256_madd_epi16(s[1], coeffs[1]);
766*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_2 = _mm256_madd_epi16(s[2], coeffs[2]);
767*77c1e3ccSAndroid Build Coastguard Worker
768*77c1e3ccSAndroid Build Coastguard Worker const __m256i res = _mm256_add_epi32(_mm256_add_epi32(res_0, res_1), res_2);
769*77c1e3ccSAndroid Build Coastguard Worker
770*77c1e3ccSAndroid Build Coastguard Worker return res;
771*77c1e3ccSAndroid Build Coastguard Worker }
772*77c1e3ccSAndroid Build Coastguard Worker
convolve_12taps(const __m256i * const s,const __m256i * const coeffs)773*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_12taps(const __m256i *const s,
774*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs) {
775*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_0 = _mm256_madd_epi16(s[0], coeffs[0]);
776*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_1 = _mm256_madd_epi16(s[1], coeffs[1]);
777*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_2 = _mm256_madd_epi16(s[2], coeffs[2]);
778*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_3 = _mm256_madd_epi16(s[3], coeffs[3]);
779*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_4 = _mm256_madd_epi16(s[4], coeffs[4]);
780*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_5 = _mm256_madd_epi16(s[5], coeffs[5]);
781*77c1e3ccSAndroid Build Coastguard Worker
782*77c1e3ccSAndroid Build Coastguard Worker const __m256i res1 = _mm256_add_epi32(_mm256_add_epi32(res_0, res_1),
783*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_2, res_3));
784*77c1e3ccSAndroid Build Coastguard Worker const __m256i res = _mm256_add_epi32(_mm256_add_epi32(res_4, res_5), res1);
785*77c1e3ccSAndroid Build Coastguard Worker
786*77c1e3ccSAndroid Build Coastguard Worker return res;
787*77c1e3ccSAndroid Build Coastguard Worker }
788*77c1e3ccSAndroid Build Coastguard Worker
convolve(const __m256i * const s,const __m256i * const coeffs)789*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve(const __m256i *const s,
790*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs) {
791*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_0 = _mm256_madd_epi16(s[0], coeffs[0]);
792*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_1 = _mm256_madd_epi16(s[1], coeffs[1]);
793*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_2 = _mm256_madd_epi16(s[2], coeffs[2]);
794*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_3 = _mm256_madd_epi16(s[3], coeffs[3]);
795*77c1e3ccSAndroid Build Coastguard Worker
796*77c1e3ccSAndroid Build Coastguard Worker const __m256i res = _mm256_add_epi32(_mm256_add_epi32(res_0, res_1),
797*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_2, res_3));
798*77c1e3ccSAndroid Build Coastguard Worker
799*77c1e3ccSAndroid Build Coastguard Worker return res;
800*77c1e3ccSAndroid Build Coastguard Worker }
801*77c1e3ccSAndroid Build Coastguard Worker
convolve_4tap(const __m256i * const s,const __m256i * const coeffs)802*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_4tap(const __m256i *const s,
803*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs) {
804*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_1 = _mm256_madd_epi16(s[0], coeffs[0]);
805*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_2 = _mm256_madd_epi16(s[1], coeffs[1]);
806*77c1e3ccSAndroid Build Coastguard Worker
807*77c1e3ccSAndroid Build Coastguard Worker const __m256i res = _mm256_add_epi32(res_1, res_2);
808*77c1e3ccSAndroid Build Coastguard Worker return res;
809*77c1e3ccSAndroid Build Coastguard Worker }
810*77c1e3ccSAndroid Build Coastguard Worker
convolve_lowbd_x(const __m256i data,const __m256i * const coeffs,const __m256i * const filt)811*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_lowbd_x(const __m256i data,
812*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs,
813*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const filt) {
814*77c1e3ccSAndroid Build Coastguard Worker __m256i s[4];
815*77c1e3ccSAndroid Build Coastguard Worker
816*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_shuffle_epi8(data, filt[0]);
817*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_shuffle_epi8(data, filt[1]);
818*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_shuffle_epi8(data, filt[2]);
819*77c1e3ccSAndroid Build Coastguard Worker s[3] = _mm256_shuffle_epi8(data, filt[3]);
820*77c1e3ccSAndroid Build Coastguard Worker
821*77c1e3ccSAndroid Build Coastguard Worker return convolve_lowbd(s, coeffs);
822*77c1e3ccSAndroid Build Coastguard Worker }
823*77c1e3ccSAndroid Build Coastguard Worker
convolve_lowbd_x_6tap(const __m256i data,const __m256i * const coeffs,const __m256i * const filt)824*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_lowbd_x_6tap(const __m256i data,
825*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs,
826*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const filt) {
827*77c1e3ccSAndroid Build Coastguard Worker __m256i s[4];
828*77c1e3ccSAndroid Build Coastguard Worker
829*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_shuffle_epi8(data, filt[0]);
830*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_shuffle_epi8(data, filt[1]);
831*77c1e3ccSAndroid Build Coastguard Worker s[2] = _mm256_shuffle_epi8(data, filt[2]);
832*77c1e3ccSAndroid Build Coastguard Worker
833*77c1e3ccSAndroid Build Coastguard Worker return convolve_lowbd_6tap(s, coeffs);
834*77c1e3ccSAndroid Build Coastguard Worker }
835*77c1e3ccSAndroid Build Coastguard Worker
convolve_lowbd_x_4tap(const __m256i data,const __m256i * const coeffs,const __m256i * const filt)836*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_lowbd_x_4tap(const __m256i data,
837*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const coeffs,
838*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const filt) {
839*77c1e3ccSAndroid Build Coastguard Worker __m256i s[2];
840*77c1e3ccSAndroid Build Coastguard Worker
841*77c1e3ccSAndroid Build Coastguard Worker s[0] = _mm256_shuffle_epi8(data, filt[0]);
842*77c1e3ccSAndroid Build Coastguard Worker s[1] = _mm256_shuffle_epi8(data, filt[1]);
843*77c1e3ccSAndroid Build Coastguard Worker
844*77c1e3ccSAndroid Build Coastguard Worker return convolve_lowbd_4tap(s, coeffs);
845*77c1e3ccSAndroid Build Coastguard Worker }
846*77c1e3ccSAndroid Build Coastguard Worker
add_store_aligned_256(CONV_BUF_TYPE * const dst,const __m256i * const res,const int do_average)847*77c1e3ccSAndroid Build Coastguard Worker static inline void add_store_aligned_256(CONV_BUF_TYPE *const dst,
848*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const res,
849*77c1e3ccSAndroid Build Coastguard Worker const int do_average) {
850*77c1e3ccSAndroid Build Coastguard Worker __m256i d;
851*77c1e3ccSAndroid Build Coastguard Worker if (do_average) {
852*77c1e3ccSAndroid Build Coastguard Worker d = _mm256_load_si256((__m256i *)dst);
853*77c1e3ccSAndroid Build Coastguard Worker d = _mm256_add_epi32(d, *res);
854*77c1e3ccSAndroid Build Coastguard Worker d = _mm256_srai_epi32(d, 1);
855*77c1e3ccSAndroid Build Coastguard Worker } else {
856*77c1e3ccSAndroid Build Coastguard Worker d = *res;
857*77c1e3ccSAndroid Build Coastguard Worker }
858*77c1e3ccSAndroid Build Coastguard Worker _mm256_store_si256((__m256i *)dst, d);
859*77c1e3ccSAndroid Build Coastguard Worker }
860*77c1e3ccSAndroid Build Coastguard Worker
comp_avg(const __m256i * const data_ref_0,const __m256i * const res_unsigned,const __m256i * const wt,const int use_dist_wtd_comp_avg)861*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i comp_avg(const __m256i *const data_ref_0,
862*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const res_unsigned,
863*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const wt,
864*77c1e3ccSAndroid Build Coastguard Worker const int use_dist_wtd_comp_avg) {
865*77c1e3ccSAndroid Build Coastguard Worker __m256i res;
866*77c1e3ccSAndroid Build Coastguard Worker if (use_dist_wtd_comp_avg) {
867*77c1e3ccSAndroid Build Coastguard Worker const __m256i data_lo = _mm256_unpacklo_epi16(*data_ref_0, *res_unsigned);
868*77c1e3ccSAndroid Build Coastguard Worker const __m256i data_hi = _mm256_unpackhi_epi16(*data_ref_0, *res_unsigned);
869*77c1e3ccSAndroid Build Coastguard Worker
870*77c1e3ccSAndroid Build Coastguard Worker const __m256i wt_res_lo = _mm256_madd_epi16(data_lo, *wt);
871*77c1e3ccSAndroid Build Coastguard Worker const __m256i wt_res_hi = _mm256_madd_epi16(data_hi, *wt);
872*77c1e3ccSAndroid Build Coastguard Worker
873*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_lo = _mm256_srai_epi32(wt_res_lo, DIST_PRECISION_BITS);
874*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_hi = _mm256_srai_epi32(wt_res_hi, DIST_PRECISION_BITS);
875*77c1e3ccSAndroid Build Coastguard Worker
876*77c1e3ccSAndroid Build Coastguard Worker res = _mm256_packs_epi32(res_lo, res_hi);
877*77c1e3ccSAndroid Build Coastguard Worker } else {
878*77c1e3ccSAndroid Build Coastguard Worker const __m256i wt_res = _mm256_add_epi16(*data_ref_0, *res_unsigned);
879*77c1e3ccSAndroid Build Coastguard Worker res = _mm256_srai_epi16(wt_res, 1);
880*77c1e3ccSAndroid Build Coastguard Worker }
881*77c1e3ccSAndroid Build Coastguard Worker return res;
882*77c1e3ccSAndroid Build Coastguard Worker }
883*77c1e3ccSAndroid Build Coastguard Worker
convolve_rounding(const __m256i * const res_unsigned,const __m256i * const offset_const,const __m256i * const round_const,const int round_shift)884*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i convolve_rounding(const __m256i *const res_unsigned,
885*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const offset_const,
886*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const round_const,
887*77c1e3ccSAndroid Build Coastguard Worker const int round_shift) {
888*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_signed = _mm256_sub_epi16(*res_unsigned, *offset_const);
889*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_round = _mm256_srai_epi16(
890*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi16(res_signed, *round_const), round_shift);
891*77c1e3ccSAndroid Build Coastguard Worker return res_round;
892*77c1e3ccSAndroid Build Coastguard Worker }
893*77c1e3ccSAndroid Build Coastguard Worker
highbd_comp_avg(const __m256i * const data_ref_0,const __m256i * const res_unsigned,const __m256i * const wt0,const __m256i * const wt1,const int use_dist_wtd_comp_avg)894*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i highbd_comp_avg(const __m256i *const data_ref_0,
895*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const res_unsigned,
896*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const wt0,
897*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const wt1,
898*77c1e3ccSAndroid Build Coastguard Worker const int use_dist_wtd_comp_avg) {
899*77c1e3ccSAndroid Build Coastguard Worker __m256i res;
900*77c1e3ccSAndroid Build Coastguard Worker if (use_dist_wtd_comp_avg) {
901*77c1e3ccSAndroid Build Coastguard Worker const __m256i wt0_res = _mm256_mullo_epi32(*data_ref_0, *wt0);
902*77c1e3ccSAndroid Build Coastguard Worker const __m256i wt1_res = _mm256_mullo_epi32(*res_unsigned, *wt1);
903*77c1e3ccSAndroid Build Coastguard Worker const __m256i wt_res = _mm256_add_epi32(wt0_res, wt1_res);
904*77c1e3ccSAndroid Build Coastguard Worker res = _mm256_srai_epi32(wt_res, DIST_PRECISION_BITS);
905*77c1e3ccSAndroid Build Coastguard Worker } else {
906*77c1e3ccSAndroid Build Coastguard Worker const __m256i wt_res = _mm256_add_epi32(*data_ref_0, *res_unsigned);
907*77c1e3ccSAndroid Build Coastguard Worker res = _mm256_srai_epi32(wt_res, 1);
908*77c1e3ccSAndroid Build Coastguard Worker }
909*77c1e3ccSAndroid Build Coastguard Worker return res;
910*77c1e3ccSAndroid Build Coastguard Worker }
911*77c1e3ccSAndroid Build Coastguard Worker
highbd_convolve_rounding(const __m256i * const res_unsigned,const __m256i * const offset_const,const __m256i * const round_const,const int round_shift)912*77c1e3ccSAndroid Build Coastguard Worker static inline __m256i highbd_convolve_rounding(
913*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const res_unsigned, const __m256i *const offset_const,
914*77c1e3ccSAndroid Build Coastguard Worker const __m256i *const round_const, const int round_shift) {
915*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_signed = _mm256_sub_epi32(*res_unsigned, *offset_const);
916*77c1e3ccSAndroid Build Coastguard Worker const __m256i res_round = _mm256_srai_epi32(
917*77c1e3ccSAndroid Build Coastguard Worker _mm256_add_epi32(res_signed, *round_const), round_shift);
918*77c1e3ccSAndroid Build Coastguard Worker
919*77c1e3ccSAndroid Build Coastguard Worker return res_round;
920*77c1e3ccSAndroid Build Coastguard Worker }
921*77c1e3ccSAndroid Build Coastguard Worker
922*77c1e3ccSAndroid Build Coastguard Worker #endif // AOM_AOM_DSP_X86_CONVOLVE_AVX2_H_
923