xref: /aosp_15_r20/external/libaom/aom_dsp/arm/sse_neon.c (revision 77c1e3ccc04c968bd2bc212e87364f250e820521)
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