1*77c1e3ccSAndroid Build Coastguard Worker /*
2*77c1e3ccSAndroid Build Coastguard Worker * Copyright (c) 2020, 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 #include <arm_neon.h>
13*77c1e3ccSAndroid Build Coastguard Worker
14*77c1e3ccSAndroid Build Coastguard Worker #include "config/aom_dsp_rtcd.h"
15*77c1e3ccSAndroid Build Coastguard Worker #include "aom_dsp/arm/mem_neon.h"
16*77c1e3ccSAndroid Build Coastguard Worker #include "aom_dsp/arm/sum_neon.h"
17*77c1e3ccSAndroid Build Coastguard Worker
sse_16x1_neon(const uint8_t * src,const uint8_t * ref,uint32x4_t * sse)18*77c1e3ccSAndroid Build Coastguard Worker static inline void sse_16x1_neon(const uint8_t *src, const uint8_t *ref,
19*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t *sse) {
20*77c1e3ccSAndroid Build Coastguard Worker uint8x16_t s = vld1q_u8(src);
21*77c1e3ccSAndroid Build Coastguard Worker uint8x16_t r = vld1q_u8(ref);
22*77c1e3ccSAndroid Build Coastguard Worker
23*77c1e3ccSAndroid Build Coastguard Worker uint8x16_t abs_diff = vabdq_u8(s, r);
24*77c1e3ccSAndroid Build Coastguard Worker uint8x8_t abs_diff_lo = vget_low_u8(abs_diff);
25*77c1e3ccSAndroid Build Coastguard Worker uint8x8_t abs_diff_hi = vget_high_u8(abs_diff);
26*77c1e3ccSAndroid Build Coastguard Worker
27*77c1e3ccSAndroid Build Coastguard Worker *sse = vpadalq_u16(*sse, vmull_u8(abs_diff_lo, abs_diff_lo));
28*77c1e3ccSAndroid Build Coastguard Worker *sse = vpadalq_u16(*sse, vmull_u8(abs_diff_hi, abs_diff_hi));
29*77c1e3ccSAndroid Build Coastguard Worker }
30*77c1e3ccSAndroid Build Coastguard Worker
sse_8x1_neon(const uint8_t * src,const uint8_t * ref,uint32x4_t * sse)31*77c1e3ccSAndroid Build Coastguard Worker static inline void sse_8x1_neon(const uint8_t *src, const uint8_t *ref,
32*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t *sse) {
33*77c1e3ccSAndroid Build Coastguard Worker uint8x8_t s = vld1_u8(src);
34*77c1e3ccSAndroid Build Coastguard Worker uint8x8_t r = vld1_u8(ref);
35*77c1e3ccSAndroid Build Coastguard Worker
36*77c1e3ccSAndroid Build Coastguard Worker uint8x8_t abs_diff = vabd_u8(s, r);
37*77c1e3ccSAndroid Build Coastguard Worker
38*77c1e3ccSAndroid Build Coastguard Worker *sse = vpadalq_u16(*sse, vmull_u8(abs_diff, abs_diff));
39*77c1e3ccSAndroid Build Coastguard Worker }
40*77c1e3ccSAndroid Build Coastguard Worker
sse_4x2_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,uint32x4_t * sse)41*77c1e3ccSAndroid Build Coastguard Worker static inline void sse_4x2_neon(const uint8_t *src, int src_stride,
42*77c1e3ccSAndroid Build Coastguard Worker const uint8_t *ref, int ref_stride,
43*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t *sse) {
44*77c1e3ccSAndroid Build Coastguard Worker uint8x8_t s = load_unaligned_u8(src, src_stride);
45*77c1e3ccSAndroid Build Coastguard Worker uint8x8_t r = load_unaligned_u8(ref, ref_stride);
46*77c1e3ccSAndroid Build Coastguard Worker
47*77c1e3ccSAndroid Build Coastguard Worker uint8x8_t abs_diff = vabd_u8(s, r);
48*77c1e3ccSAndroid Build Coastguard Worker
49*77c1e3ccSAndroid Build Coastguard Worker *sse = vpadalq_u16(*sse, vmull_u8(abs_diff, abs_diff));
50*77c1e3ccSAndroid Build Coastguard Worker }
51*77c1e3ccSAndroid Build Coastguard Worker
sse_wxh_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,int width,int height)52*77c1e3ccSAndroid Build Coastguard Worker static inline uint32_t sse_wxh_neon(const uint8_t *src, int src_stride,
53*77c1e3ccSAndroid Build Coastguard Worker const uint8_t *ref, int ref_stride,
54*77c1e3ccSAndroid Build Coastguard Worker int width, int height) {
55*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t sse = vdupq_n_u32(0);
56*77c1e3ccSAndroid Build Coastguard Worker
57*77c1e3ccSAndroid Build Coastguard Worker if ((width & 0x07) && ((width & 0x07) < 5)) {
58*77c1e3ccSAndroid Build Coastguard Worker int i = height;
59*77c1e3ccSAndroid Build Coastguard Worker do {
60*77c1e3ccSAndroid Build Coastguard Worker int j = 0;
61*77c1e3ccSAndroid Build Coastguard Worker do {
62*77c1e3ccSAndroid Build Coastguard Worker sse_8x1_neon(src + j, ref + j, &sse);
63*77c1e3ccSAndroid Build Coastguard Worker sse_8x1_neon(src + j + src_stride, ref + j + ref_stride, &sse);
64*77c1e3ccSAndroid Build Coastguard Worker j += 8;
65*77c1e3ccSAndroid Build Coastguard Worker } while (j + 4 < width);
66*77c1e3ccSAndroid Build Coastguard Worker
67*77c1e3ccSAndroid Build Coastguard Worker sse_4x2_neon(src + j, src_stride, ref + j, ref_stride, &sse);
68*77c1e3ccSAndroid Build Coastguard Worker src += 2 * src_stride;
69*77c1e3ccSAndroid Build Coastguard Worker ref += 2 * ref_stride;
70*77c1e3ccSAndroid Build Coastguard Worker i -= 2;
71*77c1e3ccSAndroid Build Coastguard Worker } while (i != 0);
72*77c1e3ccSAndroid Build Coastguard Worker } else {
73*77c1e3ccSAndroid Build Coastguard Worker int i = height;
74*77c1e3ccSAndroid Build Coastguard Worker do {
75*77c1e3ccSAndroid Build Coastguard Worker int j = 0;
76*77c1e3ccSAndroid Build Coastguard Worker do {
77*77c1e3ccSAndroid Build Coastguard Worker sse_8x1_neon(src + j, ref + j, &sse);
78*77c1e3ccSAndroid Build Coastguard Worker j += 8;
79*77c1e3ccSAndroid Build Coastguard Worker } while (j < width);
80*77c1e3ccSAndroid Build Coastguard Worker
81*77c1e3ccSAndroid Build Coastguard Worker src += src_stride;
82*77c1e3ccSAndroid Build Coastguard Worker ref += ref_stride;
83*77c1e3ccSAndroid Build Coastguard Worker } while (--i != 0);
84*77c1e3ccSAndroid Build Coastguard Worker }
85*77c1e3ccSAndroid Build Coastguard Worker return horizontal_add_u32x4(sse);
86*77c1e3ccSAndroid Build Coastguard Worker }
87*77c1e3ccSAndroid Build Coastguard Worker
sse_128xh_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,int height)88*77c1e3ccSAndroid Build Coastguard Worker static inline uint32_t sse_128xh_neon(const uint8_t *src, int src_stride,
89*77c1e3ccSAndroid Build Coastguard Worker const uint8_t *ref, int ref_stride,
90*77c1e3ccSAndroid Build Coastguard Worker int height) {
91*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t sse[2] = { vdupq_n_u32(0), vdupq_n_u32(0) };
92*77c1e3ccSAndroid Build Coastguard Worker
93*77c1e3ccSAndroid Build Coastguard Worker int i = height;
94*77c1e3ccSAndroid Build Coastguard Worker do {
95*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src, ref, &sse[0]);
96*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 16, ref + 16, &sse[1]);
97*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 32, ref + 32, &sse[0]);
98*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 48, ref + 48, &sse[1]);
99*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 64, ref + 64, &sse[0]);
100*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 80, ref + 80, &sse[1]);
101*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 96, ref + 96, &sse[0]);
102*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 112, ref + 112, &sse[1]);
103*77c1e3ccSAndroid Build Coastguard Worker
104*77c1e3ccSAndroid Build Coastguard Worker src += src_stride;
105*77c1e3ccSAndroid Build Coastguard Worker ref += ref_stride;
106*77c1e3ccSAndroid Build Coastguard Worker } while (--i != 0);
107*77c1e3ccSAndroid Build Coastguard Worker
108*77c1e3ccSAndroid Build Coastguard Worker return horizontal_add_u32x4(vaddq_u32(sse[0], sse[1]));
109*77c1e3ccSAndroid Build Coastguard Worker }
110*77c1e3ccSAndroid Build Coastguard Worker
sse_64xh_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,int height)111*77c1e3ccSAndroid Build Coastguard Worker static inline uint32_t sse_64xh_neon(const uint8_t *src, int src_stride,
112*77c1e3ccSAndroid Build Coastguard Worker const uint8_t *ref, int ref_stride,
113*77c1e3ccSAndroid Build Coastguard Worker int height) {
114*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t sse[2] = { vdupq_n_u32(0), vdupq_n_u32(0) };
115*77c1e3ccSAndroid Build Coastguard Worker
116*77c1e3ccSAndroid Build Coastguard Worker int i = height;
117*77c1e3ccSAndroid Build Coastguard Worker do {
118*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src, ref, &sse[0]);
119*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 16, ref + 16, &sse[1]);
120*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 32, ref + 32, &sse[0]);
121*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 48, ref + 48, &sse[1]);
122*77c1e3ccSAndroid Build Coastguard Worker
123*77c1e3ccSAndroid Build Coastguard Worker src += src_stride;
124*77c1e3ccSAndroid Build Coastguard Worker ref += ref_stride;
125*77c1e3ccSAndroid Build Coastguard Worker } while (--i != 0);
126*77c1e3ccSAndroid Build Coastguard Worker
127*77c1e3ccSAndroid Build Coastguard Worker return horizontal_add_u32x4(vaddq_u32(sse[0], sse[1]));
128*77c1e3ccSAndroid Build Coastguard Worker }
129*77c1e3ccSAndroid Build Coastguard Worker
sse_32xh_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,int height)130*77c1e3ccSAndroid Build Coastguard Worker static inline uint32_t sse_32xh_neon(const uint8_t *src, int src_stride,
131*77c1e3ccSAndroid Build Coastguard Worker const uint8_t *ref, int ref_stride,
132*77c1e3ccSAndroid Build Coastguard Worker int height) {
133*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t sse[2] = { vdupq_n_u32(0), vdupq_n_u32(0) };
134*77c1e3ccSAndroid Build Coastguard Worker
135*77c1e3ccSAndroid Build Coastguard Worker int i = height;
136*77c1e3ccSAndroid Build Coastguard Worker do {
137*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src, ref, &sse[0]);
138*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src + 16, ref + 16, &sse[1]);
139*77c1e3ccSAndroid Build Coastguard Worker
140*77c1e3ccSAndroid Build Coastguard Worker src += src_stride;
141*77c1e3ccSAndroid Build Coastguard Worker ref += ref_stride;
142*77c1e3ccSAndroid Build Coastguard Worker } while (--i != 0);
143*77c1e3ccSAndroid Build Coastguard Worker
144*77c1e3ccSAndroid Build Coastguard Worker return horizontal_add_u32x4(vaddq_u32(sse[0], sse[1]));
145*77c1e3ccSAndroid Build Coastguard Worker }
146*77c1e3ccSAndroid Build Coastguard Worker
sse_16xh_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,int height)147*77c1e3ccSAndroid Build Coastguard Worker static inline uint32_t sse_16xh_neon(const uint8_t *src, int src_stride,
148*77c1e3ccSAndroid Build Coastguard Worker const uint8_t *ref, int ref_stride,
149*77c1e3ccSAndroid Build Coastguard Worker int height) {
150*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t sse[2] = { vdupq_n_u32(0), vdupq_n_u32(0) };
151*77c1e3ccSAndroid Build Coastguard Worker
152*77c1e3ccSAndroid Build Coastguard Worker int i = height;
153*77c1e3ccSAndroid Build Coastguard Worker do {
154*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src, ref, &sse[0]);
155*77c1e3ccSAndroid Build Coastguard Worker src += src_stride;
156*77c1e3ccSAndroid Build Coastguard Worker ref += ref_stride;
157*77c1e3ccSAndroid Build Coastguard Worker sse_16x1_neon(src, ref, &sse[1]);
158*77c1e3ccSAndroid Build Coastguard Worker src += src_stride;
159*77c1e3ccSAndroid Build Coastguard Worker ref += ref_stride;
160*77c1e3ccSAndroid Build Coastguard Worker i -= 2;
161*77c1e3ccSAndroid Build Coastguard Worker } while (i != 0);
162*77c1e3ccSAndroid Build Coastguard Worker
163*77c1e3ccSAndroid Build Coastguard Worker return horizontal_add_u32x4(vaddq_u32(sse[0], sse[1]));
164*77c1e3ccSAndroid Build Coastguard Worker }
165*77c1e3ccSAndroid Build Coastguard Worker
sse_8xh_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,int height)166*77c1e3ccSAndroid Build Coastguard Worker static inline uint32_t sse_8xh_neon(const uint8_t *src, int src_stride,
167*77c1e3ccSAndroid Build Coastguard Worker const uint8_t *ref, int ref_stride,
168*77c1e3ccSAndroid Build Coastguard Worker int height) {
169*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t sse = vdupq_n_u32(0);
170*77c1e3ccSAndroid Build Coastguard Worker
171*77c1e3ccSAndroid Build Coastguard Worker int i = height;
172*77c1e3ccSAndroid Build Coastguard Worker do {
173*77c1e3ccSAndroid Build Coastguard Worker sse_8x1_neon(src, ref, &sse);
174*77c1e3ccSAndroid Build Coastguard Worker
175*77c1e3ccSAndroid Build Coastguard Worker src += src_stride;
176*77c1e3ccSAndroid Build Coastguard Worker ref += ref_stride;
177*77c1e3ccSAndroid Build Coastguard Worker } while (--i != 0);
178*77c1e3ccSAndroid Build Coastguard Worker
179*77c1e3ccSAndroid Build Coastguard Worker return horizontal_add_u32x4(sse);
180*77c1e3ccSAndroid Build Coastguard Worker }
181*77c1e3ccSAndroid Build Coastguard Worker
sse_4xh_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,int height)182*77c1e3ccSAndroid Build Coastguard Worker static inline uint32_t sse_4xh_neon(const uint8_t *src, int src_stride,
183*77c1e3ccSAndroid Build Coastguard Worker const uint8_t *ref, int ref_stride,
184*77c1e3ccSAndroid Build Coastguard Worker int height) {
185*77c1e3ccSAndroid Build Coastguard Worker uint32x4_t sse = vdupq_n_u32(0);
186*77c1e3ccSAndroid Build Coastguard Worker
187*77c1e3ccSAndroid Build Coastguard Worker int i = height;
188*77c1e3ccSAndroid Build Coastguard Worker do {
189*77c1e3ccSAndroid Build Coastguard Worker sse_4x2_neon(src, src_stride, ref, ref_stride, &sse);
190*77c1e3ccSAndroid Build Coastguard Worker
191*77c1e3ccSAndroid Build Coastguard Worker src += 2 * src_stride;
192*77c1e3ccSAndroid Build Coastguard Worker ref += 2 * ref_stride;
193*77c1e3ccSAndroid Build Coastguard Worker i -= 2;
194*77c1e3ccSAndroid Build Coastguard Worker } while (i != 0);
195*77c1e3ccSAndroid Build Coastguard Worker
196*77c1e3ccSAndroid Build Coastguard Worker return horizontal_add_u32x4(sse);
197*77c1e3ccSAndroid Build Coastguard Worker }
198*77c1e3ccSAndroid Build Coastguard Worker
aom_sse_neon(const uint8_t * src,int src_stride,const uint8_t * ref,int ref_stride,int width,int height)199*77c1e3ccSAndroid Build Coastguard Worker int64_t aom_sse_neon(const uint8_t *src, int src_stride, const uint8_t *ref,
200*77c1e3ccSAndroid Build Coastguard Worker int ref_stride, int width, int height) {
201*77c1e3ccSAndroid Build Coastguard Worker switch (width) {
202*77c1e3ccSAndroid Build Coastguard Worker case 4: return sse_4xh_neon(src, src_stride, ref, ref_stride, height);
203*77c1e3ccSAndroid Build Coastguard Worker case 8: return sse_8xh_neon(src, src_stride, ref, ref_stride, height);
204*77c1e3ccSAndroid Build Coastguard Worker case 16: return sse_16xh_neon(src, src_stride, ref, ref_stride, height);
205*77c1e3ccSAndroid Build Coastguard Worker case 32: return sse_32xh_neon(src, src_stride, ref, ref_stride, height);
206*77c1e3ccSAndroid Build Coastguard Worker case 64: return sse_64xh_neon(src, src_stride, ref, ref_stride, height);
207*77c1e3ccSAndroid Build Coastguard Worker case 128: return sse_128xh_neon(src, src_stride, ref, ref_stride, height);
208*77c1e3ccSAndroid Build Coastguard Worker default:
209*77c1e3ccSAndroid Build Coastguard Worker return sse_wxh_neon(src, src_stride, ref, ref_stride, width, height);
210*77c1e3ccSAndroid Build Coastguard Worker }
211*77c1e3ccSAndroid Build Coastguard Worker }
212