1*4bdc9457SAndroid Build Coastguard Worker // Auto-generated file. Do not edit!
2*4bdc9457SAndroid Build Coastguard Worker // Template: src/qs8-dwconv/unipass-neon-mul16.c.in
3*4bdc9457SAndroid Build Coastguard Worker // Generator: tools/xngen
4*4bdc9457SAndroid Build Coastguard Worker //
5*4bdc9457SAndroid Build Coastguard Worker // Copyright 2020 Google LLC
6*4bdc9457SAndroid Build Coastguard Worker //
7*4bdc9457SAndroid Build Coastguard Worker // This source code is licensed under the BSD-style license found in the
8*4bdc9457SAndroid Build Coastguard Worker // LICENSE file in the root directory of this source tree.
9*4bdc9457SAndroid Build Coastguard Worker
10*4bdc9457SAndroid Build Coastguard Worker #include <assert.h>
11*4bdc9457SAndroid Build Coastguard Worker
12*4bdc9457SAndroid Build Coastguard Worker #include <arm_neon.h>
13*4bdc9457SAndroid Build Coastguard Worker
14*4bdc9457SAndroid Build Coastguard Worker #include <xnnpack/dwconv.h>
15*4bdc9457SAndroid Build Coastguard Worker #include <xnnpack/intrinsics-polyfill.h>
16*4bdc9457SAndroid Build Coastguard Worker
17*4bdc9457SAndroid Build Coastguard Worker
xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16(size_t channels,size_t output_width,const uint8_t ** input,const void * weights,uint8_t * output,size_t input_stride,size_t output_increment,size_t input_offset,const uint8_t * zero,const union xnn_qu8_conv_minmax_params params[restrict XNN_MIN_ELEMENTS (1)])18*4bdc9457SAndroid Build Coastguard Worker void xnn_qu8_dwconv_minmax_fp32_ukernel_up32x25__neonv8_mul16(
19*4bdc9457SAndroid Build Coastguard Worker size_t channels,
20*4bdc9457SAndroid Build Coastguard Worker size_t output_width,
21*4bdc9457SAndroid Build Coastguard Worker const uint8_t** input,
22*4bdc9457SAndroid Build Coastguard Worker const void* weights,
23*4bdc9457SAndroid Build Coastguard Worker uint8_t* output,
24*4bdc9457SAndroid Build Coastguard Worker size_t input_stride,
25*4bdc9457SAndroid Build Coastguard Worker size_t output_increment,
26*4bdc9457SAndroid Build Coastguard Worker size_t input_offset,
27*4bdc9457SAndroid Build Coastguard Worker const uint8_t* zero,
28*4bdc9457SAndroid Build Coastguard Worker const union xnn_qu8_conv_minmax_params params[restrict XNN_MIN_ELEMENTS(1)]) XNN_OOB_READS
29*4bdc9457SAndroid Build Coastguard Worker {
30*4bdc9457SAndroid Build Coastguard Worker assert(channels != 0);
31*4bdc9457SAndroid Build Coastguard Worker assert(output_width != 0);
32*4bdc9457SAndroid Build Coastguard Worker
33*4bdc9457SAndroid Build Coastguard Worker const uint8x8_t vkernel_zero_point = vld1_dup_u8(params->fp32_neonv8.kernel_zero_point);
34*4bdc9457SAndroid Build Coastguard Worker const float32x4_t vscale = vld1q_dup_f32(¶ms->fp32_neonv8.scale);
35*4bdc9457SAndroid Build Coastguard Worker const int16x8_t voutput_zero_point = vld1q_dup_s16(¶ms->fp32_neonv8.output_zero_point);
36*4bdc9457SAndroid Build Coastguard Worker const uint8x16_t voutput_min = vld1q_dup_u8(¶ms->fp32_neonv8.output_min);
37*4bdc9457SAndroid Build Coastguard Worker const uint8x16_t voutput_max = vld1q_dup_u8(¶ms->fp32_neonv8.output_max);
38*4bdc9457SAndroid Build Coastguard Worker do {
39*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i0 = input[0];
40*4bdc9457SAndroid Build Coastguard Worker assert(i0 != NULL);
41*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i0 != zero) {
42*4bdc9457SAndroid Build Coastguard Worker i0 = (const uint8_t*) ((uintptr_t) i0 + input_offset);
43*4bdc9457SAndroid Build Coastguard Worker }
44*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i1 = input[1];
45*4bdc9457SAndroid Build Coastguard Worker assert(i1 != NULL);
46*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i1 != zero) {
47*4bdc9457SAndroid Build Coastguard Worker i1 = (const uint8_t*) ((uintptr_t) i1 + input_offset);
48*4bdc9457SAndroid Build Coastguard Worker }
49*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i2 = input[2];
50*4bdc9457SAndroid Build Coastguard Worker assert(i2 != NULL);
51*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i2 != zero) {
52*4bdc9457SAndroid Build Coastguard Worker i2 = (const uint8_t*) ((uintptr_t) i2 + input_offset);
53*4bdc9457SAndroid Build Coastguard Worker }
54*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i3 = input[3];
55*4bdc9457SAndroid Build Coastguard Worker assert(i3 != NULL);
56*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i3 != zero) {
57*4bdc9457SAndroid Build Coastguard Worker i3 = (const uint8_t*) ((uintptr_t) i3 + input_offset);
58*4bdc9457SAndroid Build Coastguard Worker }
59*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i4 = input[4];
60*4bdc9457SAndroid Build Coastguard Worker assert(i4 != NULL);
61*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i4 != zero) {
62*4bdc9457SAndroid Build Coastguard Worker i4 = (const uint8_t*) ((uintptr_t) i4 + input_offset);
63*4bdc9457SAndroid Build Coastguard Worker }
64*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i5 = input[5];
65*4bdc9457SAndroid Build Coastguard Worker assert(i5 != NULL);
66*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i5 != zero) {
67*4bdc9457SAndroid Build Coastguard Worker i5 = (const uint8_t*) ((uintptr_t) i5 + input_offset);
68*4bdc9457SAndroid Build Coastguard Worker }
69*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i6 = input[6];
70*4bdc9457SAndroid Build Coastguard Worker assert(i6 != NULL);
71*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i6 != zero) {
72*4bdc9457SAndroid Build Coastguard Worker i6 = (const uint8_t*) ((uintptr_t) i6 + input_offset);
73*4bdc9457SAndroid Build Coastguard Worker }
74*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i7 = input[7];
75*4bdc9457SAndroid Build Coastguard Worker assert(i7 != NULL);
76*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i7 != zero) {
77*4bdc9457SAndroid Build Coastguard Worker i7 = (const uint8_t*) ((uintptr_t) i7 + input_offset);
78*4bdc9457SAndroid Build Coastguard Worker }
79*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i8 = input[8];
80*4bdc9457SAndroid Build Coastguard Worker assert(i8 != NULL);
81*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i8 != zero) {
82*4bdc9457SAndroid Build Coastguard Worker i8 = (const uint8_t*) ((uintptr_t) i8 + input_offset);
83*4bdc9457SAndroid Build Coastguard Worker }
84*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i9 = input[9];
85*4bdc9457SAndroid Build Coastguard Worker assert(i9 != NULL);
86*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i9 != zero) {
87*4bdc9457SAndroid Build Coastguard Worker i9 = (const uint8_t*) ((uintptr_t) i9 + input_offset);
88*4bdc9457SAndroid Build Coastguard Worker }
89*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i10 = input[10];
90*4bdc9457SAndroid Build Coastguard Worker assert(i10 != NULL);
91*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i10 != zero) {
92*4bdc9457SAndroid Build Coastguard Worker i10 = (const uint8_t*) ((uintptr_t) i10 + input_offset);
93*4bdc9457SAndroid Build Coastguard Worker }
94*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i11 = input[11];
95*4bdc9457SAndroid Build Coastguard Worker assert(i11 != NULL);
96*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i11 != zero) {
97*4bdc9457SAndroid Build Coastguard Worker i11 = (const uint8_t*) ((uintptr_t) i11 + input_offset);
98*4bdc9457SAndroid Build Coastguard Worker }
99*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i12 = input[12];
100*4bdc9457SAndroid Build Coastguard Worker assert(i12 != NULL);
101*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i12 != zero) {
102*4bdc9457SAndroid Build Coastguard Worker i12 = (const uint8_t*) ((uintptr_t) i12 + input_offset);
103*4bdc9457SAndroid Build Coastguard Worker }
104*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i13 = input[13];
105*4bdc9457SAndroid Build Coastguard Worker assert(i13 != NULL);
106*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i13 != zero) {
107*4bdc9457SAndroid Build Coastguard Worker i13 = (const uint8_t*) ((uintptr_t) i13 + input_offset);
108*4bdc9457SAndroid Build Coastguard Worker }
109*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i14 = input[14];
110*4bdc9457SAndroid Build Coastguard Worker assert(i14 != NULL);
111*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i14 != zero) {
112*4bdc9457SAndroid Build Coastguard Worker i14 = (const uint8_t*) ((uintptr_t) i14 + input_offset);
113*4bdc9457SAndroid Build Coastguard Worker }
114*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i15 = input[15];
115*4bdc9457SAndroid Build Coastguard Worker assert(i15 != NULL);
116*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i15 != zero) {
117*4bdc9457SAndroid Build Coastguard Worker i15 = (const uint8_t*) ((uintptr_t) i15 + input_offset);
118*4bdc9457SAndroid Build Coastguard Worker }
119*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i16 = input[16];
120*4bdc9457SAndroid Build Coastguard Worker assert(i16 != NULL);
121*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i16 != zero) {
122*4bdc9457SAndroid Build Coastguard Worker i16 = (const uint8_t*) ((uintptr_t) i16 + input_offset);
123*4bdc9457SAndroid Build Coastguard Worker }
124*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i17 = input[17];
125*4bdc9457SAndroid Build Coastguard Worker assert(i17 != NULL);
126*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i17 != zero) {
127*4bdc9457SAndroid Build Coastguard Worker i17 = (const uint8_t*) ((uintptr_t) i17 + input_offset);
128*4bdc9457SAndroid Build Coastguard Worker }
129*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i18 = input[18];
130*4bdc9457SAndroid Build Coastguard Worker assert(i18 != NULL);
131*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i18 != zero) {
132*4bdc9457SAndroid Build Coastguard Worker i18 = (const uint8_t*) ((uintptr_t) i18 + input_offset);
133*4bdc9457SAndroid Build Coastguard Worker }
134*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i19 = input[19];
135*4bdc9457SAndroid Build Coastguard Worker assert(i19 != NULL);
136*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i19 != zero) {
137*4bdc9457SAndroid Build Coastguard Worker i19 = (const uint8_t*) ((uintptr_t) i19 + input_offset);
138*4bdc9457SAndroid Build Coastguard Worker }
139*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i20 = input[20];
140*4bdc9457SAndroid Build Coastguard Worker assert(i20 != NULL);
141*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i20 != zero) {
142*4bdc9457SAndroid Build Coastguard Worker i20 = (const uint8_t*) ((uintptr_t) i20 + input_offset);
143*4bdc9457SAndroid Build Coastguard Worker }
144*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i21 = input[21];
145*4bdc9457SAndroid Build Coastguard Worker assert(i21 != NULL);
146*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i21 != zero) {
147*4bdc9457SAndroid Build Coastguard Worker i21 = (const uint8_t*) ((uintptr_t) i21 + input_offset);
148*4bdc9457SAndroid Build Coastguard Worker }
149*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i22 = input[22];
150*4bdc9457SAndroid Build Coastguard Worker assert(i22 != NULL);
151*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i22 != zero) {
152*4bdc9457SAndroid Build Coastguard Worker i22 = (const uint8_t*) ((uintptr_t) i22 + input_offset);
153*4bdc9457SAndroid Build Coastguard Worker }
154*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i23 = input[23];
155*4bdc9457SAndroid Build Coastguard Worker assert(i23 != NULL);
156*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i23 != zero) {
157*4bdc9457SAndroid Build Coastguard Worker i23 = (const uint8_t*) ((uintptr_t) i23 + input_offset);
158*4bdc9457SAndroid Build Coastguard Worker }
159*4bdc9457SAndroid Build Coastguard Worker const uint8_t* i24 = input[24];
160*4bdc9457SAndroid Build Coastguard Worker assert(i24 != NULL);
161*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(i24 != zero) {
162*4bdc9457SAndroid Build Coastguard Worker i24 = (const uint8_t*) ((uintptr_t) i24 + input_offset);
163*4bdc9457SAndroid Build Coastguard Worker }
164*4bdc9457SAndroid Build Coastguard Worker input = (const uint8_t**) ((uintptr_t) input + input_stride);
165*4bdc9457SAndroid Build Coastguard Worker
166*4bdc9457SAndroid Build Coastguard Worker size_t c = channels;
167*4bdc9457SAndroid Build Coastguard Worker const void* w = weights;
168*4bdc9457SAndroid Build Coastguard Worker for (; c >= 32; c -= 32) {
169*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc0123 = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
170*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc4567 = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
171*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc89AB = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
172*4bdc9457SAndroid Build Coastguard Worker int32x4_t vaccCDEF = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
173*4bdc9457SAndroid Build Coastguard Worker int32x4_t vaccGHIJ = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
174*4bdc9457SAndroid Build Coastguard Worker int32x4_t vaccKLMN = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
175*4bdc9457SAndroid Build Coastguard Worker int32x4_t vaccOPQR = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
176*4bdc9457SAndroid Build Coastguard Worker int32x4_t vaccSTUV = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
177*4bdc9457SAndroid Build Coastguard Worker
178*4bdc9457SAndroid Build Coastguard Worker
179*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi0x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i0))); i0 += 8;
180*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk0x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
181*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi0x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i0))); i0 += 8;
182*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk0x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
183*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi0xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i0))); i0 += 8;
184*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk0xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
185*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi0xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i0))); i0 += 8;
186*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk0xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
187*4bdc9457SAndroid Build Coastguard Worker
188*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi0x01234567), vget_low_s16(vk0x01234567));
189*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi0x01234567), vget_high_s16(vk0x01234567));
190*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi0x89ABCDEF), vget_low_s16(vk0x89ABCDEF));
191*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi0x89ABCDEF), vget_high_s16(vk0x89ABCDEF));
192*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi0xGHIJKLMN), vget_low_s16(vk0xGHIJKLMN));
193*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi0xGHIJKLMN), vget_high_s16(vk0xGHIJKLMN));
194*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi0xOPQRSTUV), vget_low_s16(vk0xOPQRSTUV));
195*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi0xOPQRSTUV), vget_high_s16(vk0xOPQRSTUV));
196*4bdc9457SAndroid Build Coastguard Worker
197*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi1x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i1))); i1 += 8;
198*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk1x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
199*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi1x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i1))); i1 += 8;
200*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk1x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
201*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi1xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i1))); i1 += 8;
202*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk1xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
203*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi1xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i1))); i1 += 8;
204*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk1xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
205*4bdc9457SAndroid Build Coastguard Worker
206*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi1x01234567), vget_low_s16(vk1x01234567));
207*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi1x01234567), vget_high_s16(vk1x01234567));
208*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi1x89ABCDEF), vget_low_s16(vk1x89ABCDEF));
209*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi1x89ABCDEF), vget_high_s16(vk1x89ABCDEF));
210*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi1xGHIJKLMN), vget_low_s16(vk1xGHIJKLMN));
211*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi1xGHIJKLMN), vget_high_s16(vk1xGHIJKLMN));
212*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi1xOPQRSTUV), vget_low_s16(vk1xOPQRSTUV));
213*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi1xOPQRSTUV), vget_high_s16(vk1xOPQRSTUV));
214*4bdc9457SAndroid Build Coastguard Worker
215*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi2x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i2))); i2 += 8;
216*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk2x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
217*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi2x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i2))); i2 += 8;
218*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk2x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
219*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi2xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i2))); i2 += 8;
220*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk2xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
221*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi2xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i2))); i2 += 8;
222*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk2xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
223*4bdc9457SAndroid Build Coastguard Worker
224*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi2x01234567), vget_low_s16(vk2x01234567));
225*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi2x01234567), vget_high_s16(vk2x01234567));
226*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi2x89ABCDEF), vget_low_s16(vk2x89ABCDEF));
227*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi2x89ABCDEF), vget_high_s16(vk2x89ABCDEF));
228*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi2xGHIJKLMN), vget_low_s16(vk2xGHIJKLMN));
229*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi2xGHIJKLMN), vget_high_s16(vk2xGHIJKLMN));
230*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi2xOPQRSTUV), vget_low_s16(vk2xOPQRSTUV));
231*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi2xOPQRSTUV), vget_high_s16(vk2xOPQRSTUV));
232*4bdc9457SAndroid Build Coastguard Worker
233*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi3x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i3))); i3 += 8;
234*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk3x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
235*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi3x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i3))); i3 += 8;
236*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk3x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
237*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi3xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i3))); i3 += 8;
238*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk3xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
239*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi3xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i3))); i3 += 8;
240*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk3xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
241*4bdc9457SAndroid Build Coastguard Worker
242*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi3x01234567), vget_low_s16(vk3x01234567));
243*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi3x01234567), vget_high_s16(vk3x01234567));
244*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi3x89ABCDEF), vget_low_s16(vk3x89ABCDEF));
245*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi3x89ABCDEF), vget_high_s16(vk3x89ABCDEF));
246*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi3xGHIJKLMN), vget_low_s16(vk3xGHIJKLMN));
247*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi3xGHIJKLMN), vget_high_s16(vk3xGHIJKLMN));
248*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi3xOPQRSTUV), vget_low_s16(vk3xOPQRSTUV));
249*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi3xOPQRSTUV), vget_high_s16(vk3xOPQRSTUV));
250*4bdc9457SAndroid Build Coastguard Worker
251*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi4x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i4))); i4 += 8;
252*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk4x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
253*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi4x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i4))); i4 += 8;
254*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk4x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
255*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi4xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i4))); i4 += 8;
256*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk4xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
257*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi4xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i4))); i4 += 8;
258*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk4xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
259*4bdc9457SAndroid Build Coastguard Worker
260*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi4x01234567), vget_low_s16(vk4x01234567));
261*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi4x01234567), vget_high_s16(vk4x01234567));
262*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi4x89ABCDEF), vget_low_s16(vk4x89ABCDEF));
263*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi4x89ABCDEF), vget_high_s16(vk4x89ABCDEF));
264*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi4xGHIJKLMN), vget_low_s16(vk4xGHIJKLMN));
265*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi4xGHIJKLMN), vget_high_s16(vk4xGHIJKLMN));
266*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi4xOPQRSTUV), vget_low_s16(vk4xOPQRSTUV));
267*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi4xOPQRSTUV), vget_high_s16(vk4xOPQRSTUV));
268*4bdc9457SAndroid Build Coastguard Worker
269*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi5x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i5))); i5 += 8;
270*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk5x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
271*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi5x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i5))); i5 += 8;
272*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk5x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
273*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi5xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i5))); i5 += 8;
274*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk5xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
275*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi5xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i5))); i5 += 8;
276*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk5xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
277*4bdc9457SAndroid Build Coastguard Worker
278*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi5x01234567), vget_low_s16(vk5x01234567));
279*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi5x01234567), vget_high_s16(vk5x01234567));
280*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi5x89ABCDEF), vget_low_s16(vk5x89ABCDEF));
281*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi5x89ABCDEF), vget_high_s16(vk5x89ABCDEF));
282*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi5xGHIJKLMN), vget_low_s16(vk5xGHIJKLMN));
283*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi5xGHIJKLMN), vget_high_s16(vk5xGHIJKLMN));
284*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi5xOPQRSTUV), vget_low_s16(vk5xOPQRSTUV));
285*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi5xOPQRSTUV), vget_high_s16(vk5xOPQRSTUV));
286*4bdc9457SAndroid Build Coastguard Worker
287*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi6x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i6))); i6 += 8;
288*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk6x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
289*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi6x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i6))); i6 += 8;
290*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk6x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
291*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi6xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i6))); i6 += 8;
292*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk6xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
293*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi6xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i6))); i6 += 8;
294*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk6xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
295*4bdc9457SAndroid Build Coastguard Worker
296*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi6x01234567), vget_low_s16(vk6x01234567));
297*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi6x01234567), vget_high_s16(vk6x01234567));
298*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi6x89ABCDEF), vget_low_s16(vk6x89ABCDEF));
299*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi6x89ABCDEF), vget_high_s16(vk6x89ABCDEF));
300*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi6xGHIJKLMN), vget_low_s16(vk6xGHIJKLMN));
301*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi6xGHIJKLMN), vget_high_s16(vk6xGHIJKLMN));
302*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi6xOPQRSTUV), vget_low_s16(vk6xOPQRSTUV));
303*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi6xOPQRSTUV), vget_high_s16(vk6xOPQRSTUV));
304*4bdc9457SAndroid Build Coastguard Worker
305*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi7x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i7))); i7 += 8;
306*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk7x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
307*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi7x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i7))); i7 += 8;
308*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk7x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
309*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi7xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i7))); i7 += 8;
310*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk7xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
311*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi7xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i7))); i7 += 8;
312*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk7xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
313*4bdc9457SAndroid Build Coastguard Worker
314*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi7x01234567), vget_low_s16(vk7x01234567));
315*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi7x01234567), vget_high_s16(vk7x01234567));
316*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi7x89ABCDEF), vget_low_s16(vk7x89ABCDEF));
317*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi7x89ABCDEF), vget_high_s16(vk7x89ABCDEF));
318*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi7xGHIJKLMN), vget_low_s16(vk7xGHIJKLMN));
319*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi7xGHIJKLMN), vget_high_s16(vk7xGHIJKLMN));
320*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi7xOPQRSTUV), vget_low_s16(vk7xOPQRSTUV));
321*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi7xOPQRSTUV), vget_high_s16(vk7xOPQRSTUV));
322*4bdc9457SAndroid Build Coastguard Worker
323*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi8x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i8))); i8 += 8;
324*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk8x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
325*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi8x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i8))); i8 += 8;
326*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk8x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
327*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi8xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i8))); i8 += 8;
328*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk8xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
329*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi8xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i8))); i8 += 8;
330*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk8xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
331*4bdc9457SAndroid Build Coastguard Worker
332*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi8x01234567), vget_low_s16(vk8x01234567));
333*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi8x01234567), vget_high_s16(vk8x01234567));
334*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi8x89ABCDEF), vget_low_s16(vk8x89ABCDEF));
335*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi8x89ABCDEF), vget_high_s16(vk8x89ABCDEF));
336*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi8xGHIJKLMN), vget_low_s16(vk8xGHIJKLMN));
337*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi8xGHIJKLMN), vget_high_s16(vk8xGHIJKLMN));
338*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi8xOPQRSTUV), vget_low_s16(vk8xOPQRSTUV));
339*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi8xOPQRSTUV), vget_high_s16(vk8xOPQRSTUV));
340*4bdc9457SAndroid Build Coastguard Worker
341*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi9x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i9))); i9 += 8;
342*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk9x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
343*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi9x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i9))); i9 += 8;
344*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk9x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
345*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi9xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i9))); i9 += 8;
346*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk9xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
347*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi9xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i9))); i9 += 8;
348*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk9xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
349*4bdc9457SAndroid Build Coastguard Worker
350*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi9x01234567), vget_low_s16(vk9x01234567));
351*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi9x01234567), vget_high_s16(vk9x01234567));
352*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi9x89ABCDEF), vget_low_s16(vk9x89ABCDEF));
353*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi9x89ABCDEF), vget_high_s16(vk9x89ABCDEF));
354*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi9xGHIJKLMN), vget_low_s16(vk9xGHIJKLMN));
355*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi9xGHIJKLMN), vget_high_s16(vk9xGHIJKLMN));
356*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi9xOPQRSTUV), vget_low_s16(vk9xOPQRSTUV));
357*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi9xOPQRSTUV), vget_high_s16(vk9xOPQRSTUV));
358*4bdc9457SAndroid Build Coastguard Worker
359*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi10x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i10))); i10 += 8;
360*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk10x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
361*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi10x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i10))); i10 += 8;
362*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk10x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
363*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi10xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i10))); i10 += 8;
364*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk10xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
365*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi10xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i10))); i10 += 8;
366*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk10xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
367*4bdc9457SAndroid Build Coastguard Worker
368*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi10x01234567), vget_low_s16(vk10x01234567));
369*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi10x01234567), vget_high_s16(vk10x01234567));
370*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi10x89ABCDEF), vget_low_s16(vk10x89ABCDEF));
371*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi10x89ABCDEF), vget_high_s16(vk10x89ABCDEF));
372*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi10xGHIJKLMN), vget_low_s16(vk10xGHIJKLMN));
373*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi10xGHIJKLMN), vget_high_s16(vk10xGHIJKLMN));
374*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi10xOPQRSTUV), vget_low_s16(vk10xOPQRSTUV));
375*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi10xOPQRSTUV), vget_high_s16(vk10xOPQRSTUV));
376*4bdc9457SAndroid Build Coastguard Worker
377*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi11x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i11))); i11 += 8;
378*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk11x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
379*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi11x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i11))); i11 += 8;
380*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk11x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
381*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi11xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i11))); i11 += 8;
382*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk11xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
383*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi11xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i11))); i11 += 8;
384*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk11xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
385*4bdc9457SAndroid Build Coastguard Worker
386*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi11x01234567), vget_low_s16(vk11x01234567));
387*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi11x01234567), vget_high_s16(vk11x01234567));
388*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi11x89ABCDEF), vget_low_s16(vk11x89ABCDEF));
389*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi11x89ABCDEF), vget_high_s16(vk11x89ABCDEF));
390*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi11xGHIJKLMN), vget_low_s16(vk11xGHIJKLMN));
391*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi11xGHIJKLMN), vget_high_s16(vk11xGHIJKLMN));
392*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi11xOPQRSTUV), vget_low_s16(vk11xOPQRSTUV));
393*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi11xOPQRSTUV), vget_high_s16(vk11xOPQRSTUV));
394*4bdc9457SAndroid Build Coastguard Worker
395*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi12x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i12))); i12 += 8;
396*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk12x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
397*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi12x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i12))); i12 += 8;
398*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk12x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
399*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi12xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i12))); i12 += 8;
400*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk12xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
401*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi12xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i12))); i12 += 8;
402*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk12xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
403*4bdc9457SAndroid Build Coastguard Worker
404*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi12x01234567), vget_low_s16(vk12x01234567));
405*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi12x01234567), vget_high_s16(vk12x01234567));
406*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi12x89ABCDEF), vget_low_s16(vk12x89ABCDEF));
407*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi12x89ABCDEF), vget_high_s16(vk12x89ABCDEF));
408*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi12xGHIJKLMN), vget_low_s16(vk12xGHIJKLMN));
409*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi12xGHIJKLMN), vget_high_s16(vk12xGHIJKLMN));
410*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi12xOPQRSTUV), vget_low_s16(vk12xOPQRSTUV));
411*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi12xOPQRSTUV), vget_high_s16(vk12xOPQRSTUV));
412*4bdc9457SAndroid Build Coastguard Worker
413*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi13x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i13))); i13 += 8;
414*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk13x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
415*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi13x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i13))); i13 += 8;
416*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk13x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
417*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi13xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i13))); i13 += 8;
418*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk13xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
419*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi13xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i13))); i13 += 8;
420*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk13xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
421*4bdc9457SAndroid Build Coastguard Worker
422*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi13x01234567), vget_low_s16(vk13x01234567));
423*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi13x01234567), vget_high_s16(vk13x01234567));
424*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi13x89ABCDEF), vget_low_s16(vk13x89ABCDEF));
425*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi13x89ABCDEF), vget_high_s16(vk13x89ABCDEF));
426*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi13xGHIJKLMN), vget_low_s16(vk13xGHIJKLMN));
427*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi13xGHIJKLMN), vget_high_s16(vk13xGHIJKLMN));
428*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi13xOPQRSTUV), vget_low_s16(vk13xOPQRSTUV));
429*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi13xOPQRSTUV), vget_high_s16(vk13xOPQRSTUV));
430*4bdc9457SAndroid Build Coastguard Worker
431*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi14x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i14))); i14 += 8;
432*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk14x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
433*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi14x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i14))); i14 += 8;
434*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk14x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
435*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi14xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i14))); i14 += 8;
436*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk14xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
437*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi14xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i14))); i14 += 8;
438*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk14xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
439*4bdc9457SAndroid Build Coastguard Worker
440*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi14x01234567), vget_low_s16(vk14x01234567));
441*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi14x01234567), vget_high_s16(vk14x01234567));
442*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi14x89ABCDEF), vget_low_s16(vk14x89ABCDEF));
443*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi14x89ABCDEF), vget_high_s16(vk14x89ABCDEF));
444*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi14xGHIJKLMN), vget_low_s16(vk14xGHIJKLMN));
445*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi14xGHIJKLMN), vget_high_s16(vk14xGHIJKLMN));
446*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi14xOPQRSTUV), vget_low_s16(vk14xOPQRSTUV));
447*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi14xOPQRSTUV), vget_high_s16(vk14xOPQRSTUV));
448*4bdc9457SAndroid Build Coastguard Worker
449*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi15x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i15))); i15 += 8;
450*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk15x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
451*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi15x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i15))); i15 += 8;
452*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk15x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
453*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi15xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i15))); i15 += 8;
454*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk15xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
455*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi15xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i15))); i15 += 8;
456*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk15xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
457*4bdc9457SAndroid Build Coastguard Worker
458*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi15x01234567), vget_low_s16(vk15x01234567));
459*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi15x01234567), vget_high_s16(vk15x01234567));
460*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi15x89ABCDEF), vget_low_s16(vk15x89ABCDEF));
461*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi15x89ABCDEF), vget_high_s16(vk15x89ABCDEF));
462*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi15xGHIJKLMN), vget_low_s16(vk15xGHIJKLMN));
463*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi15xGHIJKLMN), vget_high_s16(vk15xGHIJKLMN));
464*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi15xOPQRSTUV), vget_low_s16(vk15xOPQRSTUV));
465*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi15xOPQRSTUV), vget_high_s16(vk15xOPQRSTUV));
466*4bdc9457SAndroid Build Coastguard Worker
467*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi16x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i16))); i16 += 8;
468*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk16x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
469*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi16x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i16))); i16 += 8;
470*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk16x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
471*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi16xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i16))); i16 += 8;
472*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk16xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
473*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi16xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i16))); i16 += 8;
474*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk16xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
475*4bdc9457SAndroid Build Coastguard Worker
476*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi16x01234567), vget_low_s16(vk16x01234567));
477*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi16x01234567), vget_high_s16(vk16x01234567));
478*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi16x89ABCDEF), vget_low_s16(vk16x89ABCDEF));
479*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi16x89ABCDEF), vget_high_s16(vk16x89ABCDEF));
480*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi16xGHIJKLMN), vget_low_s16(vk16xGHIJKLMN));
481*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi16xGHIJKLMN), vget_high_s16(vk16xGHIJKLMN));
482*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi16xOPQRSTUV), vget_low_s16(vk16xOPQRSTUV));
483*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi16xOPQRSTUV), vget_high_s16(vk16xOPQRSTUV));
484*4bdc9457SAndroid Build Coastguard Worker
485*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi17x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i17))); i17 += 8;
486*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk17x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
487*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi17x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i17))); i17 += 8;
488*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk17x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
489*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi17xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i17))); i17 += 8;
490*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk17xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
491*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi17xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i17))); i17 += 8;
492*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk17xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
493*4bdc9457SAndroid Build Coastguard Worker
494*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi17x01234567), vget_low_s16(vk17x01234567));
495*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi17x01234567), vget_high_s16(vk17x01234567));
496*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi17x89ABCDEF), vget_low_s16(vk17x89ABCDEF));
497*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi17x89ABCDEF), vget_high_s16(vk17x89ABCDEF));
498*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi17xGHIJKLMN), vget_low_s16(vk17xGHIJKLMN));
499*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi17xGHIJKLMN), vget_high_s16(vk17xGHIJKLMN));
500*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi17xOPQRSTUV), vget_low_s16(vk17xOPQRSTUV));
501*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi17xOPQRSTUV), vget_high_s16(vk17xOPQRSTUV));
502*4bdc9457SAndroid Build Coastguard Worker
503*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi18x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i18))); i18 += 8;
504*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk18x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
505*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi18x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i18))); i18 += 8;
506*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk18x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
507*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi18xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i18))); i18 += 8;
508*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk18xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
509*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi18xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i18))); i18 += 8;
510*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk18xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
511*4bdc9457SAndroid Build Coastguard Worker
512*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi18x01234567), vget_low_s16(vk18x01234567));
513*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi18x01234567), vget_high_s16(vk18x01234567));
514*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi18x89ABCDEF), vget_low_s16(vk18x89ABCDEF));
515*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi18x89ABCDEF), vget_high_s16(vk18x89ABCDEF));
516*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi18xGHIJKLMN), vget_low_s16(vk18xGHIJKLMN));
517*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi18xGHIJKLMN), vget_high_s16(vk18xGHIJKLMN));
518*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi18xOPQRSTUV), vget_low_s16(vk18xOPQRSTUV));
519*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi18xOPQRSTUV), vget_high_s16(vk18xOPQRSTUV));
520*4bdc9457SAndroid Build Coastguard Worker
521*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi19x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i19))); i19 += 8;
522*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk19x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
523*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi19x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i19))); i19 += 8;
524*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk19x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
525*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi19xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i19))); i19 += 8;
526*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk19xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
527*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi19xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i19))); i19 += 8;
528*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk19xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
529*4bdc9457SAndroid Build Coastguard Worker
530*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi19x01234567), vget_low_s16(vk19x01234567));
531*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi19x01234567), vget_high_s16(vk19x01234567));
532*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi19x89ABCDEF), vget_low_s16(vk19x89ABCDEF));
533*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi19x89ABCDEF), vget_high_s16(vk19x89ABCDEF));
534*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi19xGHIJKLMN), vget_low_s16(vk19xGHIJKLMN));
535*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi19xGHIJKLMN), vget_high_s16(vk19xGHIJKLMN));
536*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi19xOPQRSTUV), vget_low_s16(vk19xOPQRSTUV));
537*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi19xOPQRSTUV), vget_high_s16(vk19xOPQRSTUV));
538*4bdc9457SAndroid Build Coastguard Worker
539*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi20x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i20))); i20 += 8;
540*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk20x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
541*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi20x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i20))); i20 += 8;
542*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk20x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
543*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi20xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i20))); i20 += 8;
544*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk20xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
545*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi20xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i20))); i20 += 8;
546*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk20xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
547*4bdc9457SAndroid Build Coastguard Worker
548*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi20x01234567), vget_low_s16(vk20x01234567));
549*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi20x01234567), vget_high_s16(vk20x01234567));
550*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi20x89ABCDEF), vget_low_s16(vk20x89ABCDEF));
551*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi20x89ABCDEF), vget_high_s16(vk20x89ABCDEF));
552*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi20xGHIJKLMN), vget_low_s16(vk20xGHIJKLMN));
553*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi20xGHIJKLMN), vget_high_s16(vk20xGHIJKLMN));
554*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi20xOPQRSTUV), vget_low_s16(vk20xOPQRSTUV));
555*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi20xOPQRSTUV), vget_high_s16(vk20xOPQRSTUV));
556*4bdc9457SAndroid Build Coastguard Worker
557*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi21x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i21))); i21 += 8;
558*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk21x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
559*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi21x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i21))); i21 += 8;
560*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk21x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
561*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi21xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i21))); i21 += 8;
562*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk21xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
563*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi21xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i21))); i21 += 8;
564*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk21xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
565*4bdc9457SAndroid Build Coastguard Worker
566*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi21x01234567), vget_low_s16(vk21x01234567));
567*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi21x01234567), vget_high_s16(vk21x01234567));
568*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi21x89ABCDEF), vget_low_s16(vk21x89ABCDEF));
569*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi21x89ABCDEF), vget_high_s16(vk21x89ABCDEF));
570*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi21xGHIJKLMN), vget_low_s16(vk21xGHIJKLMN));
571*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi21xGHIJKLMN), vget_high_s16(vk21xGHIJKLMN));
572*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi21xOPQRSTUV), vget_low_s16(vk21xOPQRSTUV));
573*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi21xOPQRSTUV), vget_high_s16(vk21xOPQRSTUV));
574*4bdc9457SAndroid Build Coastguard Worker
575*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi22x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i22))); i22 += 8;
576*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk22x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
577*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi22x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i22))); i22 += 8;
578*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk22x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
579*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi22xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i22))); i22 += 8;
580*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk22xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
581*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi22xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i22))); i22 += 8;
582*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk22xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
583*4bdc9457SAndroid Build Coastguard Worker
584*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi22x01234567), vget_low_s16(vk22x01234567));
585*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi22x01234567), vget_high_s16(vk22x01234567));
586*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi22x89ABCDEF), vget_low_s16(vk22x89ABCDEF));
587*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi22x89ABCDEF), vget_high_s16(vk22x89ABCDEF));
588*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi22xGHIJKLMN), vget_low_s16(vk22xGHIJKLMN));
589*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi22xGHIJKLMN), vget_high_s16(vk22xGHIJKLMN));
590*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi22xOPQRSTUV), vget_low_s16(vk22xOPQRSTUV));
591*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi22xOPQRSTUV), vget_high_s16(vk22xOPQRSTUV));
592*4bdc9457SAndroid Build Coastguard Worker
593*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi23x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i23))); i23 += 8;
594*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk23x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
595*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi23x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i23))); i23 += 8;
596*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk23x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
597*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi23xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i23))); i23 += 8;
598*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk23xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
599*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi23xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i23))); i23 += 8;
600*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk23xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
601*4bdc9457SAndroid Build Coastguard Worker
602*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi23x01234567), vget_low_s16(vk23x01234567));
603*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi23x01234567), vget_high_s16(vk23x01234567));
604*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi23x89ABCDEF), vget_low_s16(vk23x89ABCDEF));
605*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi23x89ABCDEF), vget_high_s16(vk23x89ABCDEF));
606*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi23xGHIJKLMN), vget_low_s16(vk23xGHIJKLMN));
607*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi23xGHIJKLMN), vget_high_s16(vk23xGHIJKLMN));
608*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi23xOPQRSTUV), vget_low_s16(vk23xOPQRSTUV));
609*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi23xOPQRSTUV), vget_high_s16(vk23xOPQRSTUV));
610*4bdc9457SAndroid Build Coastguard Worker
611*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi24x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i24))); i24 += 8;
612*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk24x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
613*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi24x89ABCDEF = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i24))); i24 += 8;
614*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk24x89ABCDEF = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
615*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi24xGHIJKLMN = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i24))); i24 += 8;
616*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk24xGHIJKLMN = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
617*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi24xOPQRSTUV = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i24))); i24 += 8;
618*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk24xOPQRSTUV = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(w), vkernel_zero_point)); w = (const void*) ((const uint8_t*) w + 8);
619*4bdc9457SAndroid Build Coastguard Worker
620*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi24x01234567), vget_low_s16(vk24x01234567));
621*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi24x01234567), vget_high_s16(vk24x01234567));
622*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vmlal_s16(vacc89AB, vget_low_s16(vi24x89ABCDEF), vget_low_s16(vk24x89ABCDEF));
623*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vmlal_s16(vaccCDEF, vget_high_s16(vi24x89ABCDEF), vget_high_s16(vk24x89ABCDEF));
624*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vmlal_s16(vaccGHIJ, vget_low_s16(vi24xGHIJKLMN), vget_low_s16(vk24xGHIJKLMN));
625*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vmlal_s16(vaccKLMN, vget_high_s16(vi24xGHIJKLMN), vget_high_s16(vk24xGHIJKLMN));
626*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vmlal_s16(vaccOPQR, vget_low_s16(vi24xOPQRSTUV), vget_low_s16(vk24xOPQRSTUV));
627*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vmlal_s16(vaccSTUV, vget_high_s16(vi24xOPQRSTUV), vget_high_s16(vk24xOPQRSTUV));
628*4bdc9457SAndroid Build Coastguard Worker
629*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpacc0123 = vcvtq_f32_s32(vacc0123);
630*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpacc4567 = vcvtq_f32_s32(vacc4567);
631*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpacc89AB = vcvtq_f32_s32(vacc89AB);
632*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpaccCDEF = vcvtq_f32_s32(vaccCDEF);
633*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpaccGHIJ = vcvtq_f32_s32(vaccGHIJ);
634*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpaccKLMN = vcvtq_f32_s32(vaccKLMN);
635*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpaccOPQR = vcvtq_f32_s32(vaccOPQR);
636*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpaccSTUV = vcvtq_f32_s32(vaccSTUV);
637*4bdc9457SAndroid Build Coastguard Worker
638*4bdc9457SAndroid Build Coastguard Worker vfpacc0123 = vmulq_f32(vfpacc0123, vscale);
639*4bdc9457SAndroid Build Coastguard Worker vfpacc4567 = vmulq_f32(vfpacc4567, vscale);
640*4bdc9457SAndroid Build Coastguard Worker vfpacc89AB = vmulq_f32(vfpacc89AB, vscale);
641*4bdc9457SAndroid Build Coastguard Worker vfpaccCDEF = vmulq_f32(vfpaccCDEF, vscale);
642*4bdc9457SAndroid Build Coastguard Worker vfpaccGHIJ = vmulq_f32(vfpaccGHIJ, vscale);
643*4bdc9457SAndroid Build Coastguard Worker vfpaccKLMN = vmulq_f32(vfpaccKLMN, vscale);
644*4bdc9457SAndroid Build Coastguard Worker vfpaccOPQR = vmulq_f32(vfpaccOPQR, vscale);
645*4bdc9457SAndroid Build Coastguard Worker vfpaccSTUV = vmulq_f32(vfpaccSTUV, vscale);
646*4bdc9457SAndroid Build Coastguard Worker
647*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vcvtnq_s32_f32(vfpacc0123);
648*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vcvtnq_s32_f32(vfpacc4567);
649*4bdc9457SAndroid Build Coastguard Worker vacc89AB = vcvtnq_s32_f32(vfpacc89AB);
650*4bdc9457SAndroid Build Coastguard Worker vaccCDEF = vcvtnq_s32_f32(vfpaccCDEF);
651*4bdc9457SAndroid Build Coastguard Worker vaccGHIJ = vcvtnq_s32_f32(vfpaccGHIJ);
652*4bdc9457SAndroid Build Coastguard Worker vaccKLMN = vcvtnq_s32_f32(vfpaccKLMN);
653*4bdc9457SAndroid Build Coastguard Worker vaccOPQR = vcvtnq_s32_f32(vfpaccOPQR);
654*4bdc9457SAndroid Build Coastguard Worker vaccSTUV = vcvtnq_s32_f32(vfpaccSTUV);
655*4bdc9457SAndroid Build Coastguard Worker
656*4bdc9457SAndroid Build Coastguard Worker #if XNN_ARCH_ARM64
657*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc01234567 = vqmovn_high_s32(vqmovn_s32(vacc0123), vacc4567);
658*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc89ABCDEF = vqmovn_high_s32(vqmovn_s32(vacc89AB), vaccCDEF);
659*4bdc9457SAndroid Build Coastguard Worker int16x8_t vaccGHIJKLMN = vqmovn_high_s32(vqmovn_s32(vaccGHIJ), vaccKLMN);
660*4bdc9457SAndroid Build Coastguard Worker int16x8_t vaccOPQRSTUV = vqmovn_high_s32(vqmovn_s32(vaccOPQR), vaccSTUV);
661*4bdc9457SAndroid Build Coastguard Worker
662*4bdc9457SAndroid Build Coastguard Worker vacc01234567 = vqaddq_s16(vacc01234567, voutput_zero_point);
663*4bdc9457SAndroid Build Coastguard Worker vacc89ABCDEF = vqaddq_s16(vacc89ABCDEF, voutput_zero_point);
664*4bdc9457SAndroid Build Coastguard Worker vaccGHIJKLMN = vqaddq_s16(vaccGHIJKLMN, voutput_zero_point);
665*4bdc9457SAndroid Build Coastguard Worker vaccOPQRSTUV = vqaddq_s16(vaccOPQRSTUV, voutput_zero_point);
666*4bdc9457SAndroid Build Coastguard Worker
667*4bdc9457SAndroid Build Coastguard Worker uint8x16_t vout0123456789ABCDEF = vqmovun_high_s16(vqmovun_s16(vacc01234567), vacc89ABCDEF);
668*4bdc9457SAndroid Build Coastguard Worker uint8x16_t voutGHIJKLMNOPQRSTUV = vqmovun_high_s16(vqmovun_s16(vaccGHIJKLMN), vaccOPQRSTUV);
669*4bdc9457SAndroid Build Coastguard Worker #else // !XNN_ARCH_ARM64
670*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc01234567 = vcombine_s16(vqmovn_s32(vacc0123), vqmovn_s32(vacc4567));
671*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc89ABCDEF = vcombine_s16(vqmovn_s32(vacc89AB), vqmovn_s32(vaccCDEF));
672*4bdc9457SAndroid Build Coastguard Worker int16x8_t vaccGHIJKLMN = vcombine_s16(vqmovn_s32(vaccGHIJ), vqmovn_s32(vaccKLMN));
673*4bdc9457SAndroid Build Coastguard Worker int16x8_t vaccOPQRSTUV = vcombine_s16(vqmovn_s32(vaccOPQR), vqmovn_s32(vaccSTUV));
674*4bdc9457SAndroid Build Coastguard Worker
675*4bdc9457SAndroid Build Coastguard Worker vacc01234567 = vqaddq_s16(vacc01234567, voutput_zero_point);
676*4bdc9457SAndroid Build Coastguard Worker vacc89ABCDEF = vqaddq_s16(vacc89ABCDEF, voutput_zero_point);
677*4bdc9457SAndroid Build Coastguard Worker vaccGHIJKLMN = vqaddq_s16(vaccGHIJKLMN, voutput_zero_point);
678*4bdc9457SAndroid Build Coastguard Worker vaccOPQRSTUV = vqaddq_s16(vaccOPQRSTUV, voutput_zero_point);
679*4bdc9457SAndroid Build Coastguard Worker
680*4bdc9457SAndroid Build Coastguard Worker uint8x16_t vout0123456789ABCDEF = vcombine_u8(vqmovun_s16(vacc01234567), vqmovun_s16(vacc89ABCDEF));
681*4bdc9457SAndroid Build Coastguard Worker uint8x16_t voutGHIJKLMNOPQRSTUV = vcombine_u8(vqmovun_s16(vaccGHIJKLMN), vqmovun_s16(vaccOPQRSTUV));
682*4bdc9457SAndroid Build Coastguard Worker #endif // !XNN_ARCH_ARM64
683*4bdc9457SAndroid Build Coastguard Worker
684*4bdc9457SAndroid Build Coastguard Worker vout0123456789ABCDEF = vmaxq_u8(vout0123456789ABCDEF, voutput_min);
685*4bdc9457SAndroid Build Coastguard Worker voutGHIJKLMNOPQRSTUV = vmaxq_u8(voutGHIJKLMNOPQRSTUV, voutput_min);
686*4bdc9457SAndroid Build Coastguard Worker
687*4bdc9457SAndroid Build Coastguard Worker vout0123456789ABCDEF = vminq_u8(vout0123456789ABCDEF, voutput_max);
688*4bdc9457SAndroid Build Coastguard Worker voutGHIJKLMNOPQRSTUV = vminq_u8(voutGHIJKLMNOPQRSTUV, voutput_max);
689*4bdc9457SAndroid Build Coastguard Worker
690*4bdc9457SAndroid Build Coastguard Worker vst1q_u8(output, vout0123456789ABCDEF); output += 16;
691*4bdc9457SAndroid Build Coastguard Worker vst1q_u8(output, voutGHIJKLMNOPQRSTUV); output += 16;
692*4bdc9457SAndroid Build Coastguard Worker }
693*4bdc9457SAndroid Build Coastguard Worker if XNN_UNLIKELY(c != 0) {
694*4bdc9457SAndroid Build Coastguard Worker const uint8_t* k = (const uint8_t*) ((const int32_t*) w + 32);
695*4bdc9457SAndroid Build Coastguard Worker do {
696*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc0123 = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
697*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc4567 = vld1q_s32(w); w = (const void*) ((const int32_t*) w + 4);
698*4bdc9457SAndroid Build Coastguard Worker
699*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi0x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i0))); i0 += 8;
700*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk0x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8(k), vkernel_zero_point)); k += 8;
701*4bdc9457SAndroid Build Coastguard Worker
702*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi0x01234567), vget_low_s16(vk0x01234567));
703*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi0x01234567), vget_high_s16(vk0x01234567));
704*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi1x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i1))); i1 += 8;
705*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk1x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 24)), vkernel_zero_point));
706*4bdc9457SAndroid Build Coastguard Worker
707*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi1x01234567), vget_low_s16(vk1x01234567));
708*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi1x01234567), vget_high_s16(vk1x01234567));
709*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi2x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i2))); i2 += 8;
710*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk2x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 56)), vkernel_zero_point));
711*4bdc9457SAndroid Build Coastguard Worker
712*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi2x01234567), vget_low_s16(vk2x01234567));
713*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi2x01234567), vget_high_s16(vk2x01234567));
714*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi3x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i3))); i3 += 8;
715*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk3x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 88)), vkernel_zero_point));
716*4bdc9457SAndroid Build Coastguard Worker
717*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi3x01234567), vget_low_s16(vk3x01234567));
718*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi3x01234567), vget_high_s16(vk3x01234567));
719*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi4x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i4))); i4 += 8;
720*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk4x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 120)), vkernel_zero_point));
721*4bdc9457SAndroid Build Coastguard Worker
722*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi4x01234567), vget_low_s16(vk4x01234567));
723*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi4x01234567), vget_high_s16(vk4x01234567));
724*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi5x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i5))); i5 += 8;
725*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk5x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 152)), vkernel_zero_point));
726*4bdc9457SAndroid Build Coastguard Worker
727*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi5x01234567), vget_low_s16(vk5x01234567));
728*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi5x01234567), vget_high_s16(vk5x01234567));
729*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi6x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i6))); i6 += 8;
730*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk6x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 184)), vkernel_zero_point));
731*4bdc9457SAndroid Build Coastguard Worker
732*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi6x01234567), vget_low_s16(vk6x01234567));
733*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi6x01234567), vget_high_s16(vk6x01234567));
734*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi7x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i7))); i7 += 8;
735*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk7x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 216)), vkernel_zero_point));
736*4bdc9457SAndroid Build Coastguard Worker
737*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi7x01234567), vget_low_s16(vk7x01234567));
738*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi7x01234567), vget_high_s16(vk7x01234567));
739*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi8x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i8))); i8 += 8;
740*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk8x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 248)), vkernel_zero_point));
741*4bdc9457SAndroid Build Coastguard Worker
742*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi8x01234567), vget_low_s16(vk8x01234567));
743*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi8x01234567), vget_high_s16(vk8x01234567));
744*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi9x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i9))); i9 += 8;
745*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk9x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 280)), vkernel_zero_point));
746*4bdc9457SAndroid Build Coastguard Worker
747*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi9x01234567), vget_low_s16(vk9x01234567));
748*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi9x01234567), vget_high_s16(vk9x01234567));
749*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi10x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i10))); i10 += 8;
750*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk10x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 312)), vkernel_zero_point));
751*4bdc9457SAndroid Build Coastguard Worker
752*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi10x01234567), vget_low_s16(vk10x01234567));
753*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi10x01234567), vget_high_s16(vk10x01234567));
754*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi11x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i11))); i11 += 8;
755*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk11x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 344)), vkernel_zero_point));
756*4bdc9457SAndroid Build Coastguard Worker
757*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi11x01234567), vget_low_s16(vk11x01234567));
758*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi11x01234567), vget_high_s16(vk11x01234567));
759*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi12x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i12))); i12 += 8;
760*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk12x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 376)), vkernel_zero_point));
761*4bdc9457SAndroid Build Coastguard Worker
762*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi12x01234567), vget_low_s16(vk12x01234567));
763*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi12x01234567), vget_high_s16(vk12x01234567));
764*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi13x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i13))); i13 += 8;
765*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk13x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 408)), vkernel_zero_point));
766*4bdc9457SAndroid Build Coastguard Worker
767*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi13x01234567), vget_low_s16(vk13x01234567));
768*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi13x01234567), vget_high_s16(vk13x01234567));
769*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi14x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i14))); i14 += 8;
770*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk14x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 440)), vkernel_zero_point));
771*4bdc9457SAndroid Build Coastguard Worker
772*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi14x01234567), vget_low_s16(vk14x01234567));
773*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi14x01234567), vget_high_s16(vk14x01234567));
774*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi15x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i15))); i15 += 8;
775*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk15x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 472)), vkernel_zero_point));
776*4bdc9457SAndroid Build Coastguard Worker
777*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi15x01234567), vget_low_s16(vk15x01234567));
778*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi15x01234567), vget_high_s16(vk15x01234567));
779*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi16x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i16))); i16 += 8;
780*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk16x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 504)), vkernel_zero_point));
781*4bdc9457SAndroid Build Coastguard Worker
782*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi16x01234567), vget_low_s16(vk16x01234567));
783*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi16x01234567), vget_high_s16(vk16x01234567));
784*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi17x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i17))); i17 += 8;
785*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk17x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 536)), vkernel_zero_point));
786*4bdc9457SAndroid Build Coastguard Worker
787*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi17x01234567), vget_low_s16(vk17x01234567));
788*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi17x01234567), vget_high_s16(vk17x01234567));
789*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi18x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i18))); i18 += 8;
790*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk18x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 568)), vkernel_zero_point));
791*4bdc9457SAndroid Build Coastguard Worker
792*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi18x01234567), vget_low_s16(vk18x01234567));
793*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi18x01234567), vget_high_s16(vk18x01234567));
794*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi19x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i19))); i19 += 8;
795*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk19x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 600)), vkernel_zero_point));
796*4bdc9457SAndroid Build Coastguard Worker
797*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi19x01234567), vget_low_s16(vk19x01234567));
798*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi19x01234567), vget_high_s16(vk19x01234567));
799*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi20x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i20))); i20 += 8;
800*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk20x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 632)), vkernel_zero_point));
801*4bdc9457SAndroid Build Coastguard Worker
802*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi20x01234567), vget_low_s16(vk20x01234567));
803*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi20x01234567), vget_high_s16(vk20x01234567));
804*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi21x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i21))); i21 += 8;
805*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk21x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 664)), vkernel_zero_point));
806*4bdc9457SAndroid Build Coastguard Worker
807*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi21x01234567), vget_low_s16(vk21x01234567));
808*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi21x01234567), vget_high_s16(vk21x01234567));
809*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi22x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i22))); i22 += 8;
810*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk22x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 696)), vkernel_zero_point));
811*4bdc9457SAndroid Build Coastguard Worker
812*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi22x01234567), vget_low_s16(vk22x01234567));
813*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi22x01234567), vget_high_s16(vk22x01234567));
814*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi23x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i23))); i23 += 8;
815*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk23x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 728)), vkernel_zero_point));
816*4bdc9457SAndroid Build Coastguard Worker
817*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi23x01234567), vget_low_s16(vk23x01234567));
818*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi23x01234567), vget_high_s16(vk23x01234567));
819*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vi24x01234567 = vreinterpretq_s16_u16(vmovl_u8(vld1_u8(i24))); i24 += 8;
820*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vk24x01234567 = vreinterpretq_s16_u16(vsubl_u8(vld1_u8((const void*) (k + 760)), vkernel_zero_point));
821*4bdc9457SAndroid Build Coastguard Worker
822*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vmlal_s16(vacc0123, vget_low_s16(vi24x01234567), vget_low_s16(vk24x01234567));
823*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vmlal_s16(vacc4567, vget_high_s16(vi24x01234567), vget_high_s16(vk24x01234567));
824*4bdc9457SAndroid Build Coastguard Worker
825*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpacc0123 = vcvtq_f32_s32(vacc0123);
826*4bdc9457SAndroid Build Coastguard Worker float32x4_t vfpacc4567 = vcvtq_f32_s32(vacc4567);
827*4bdc9457SAndroid Build Coastguard Worker
828*4bdc9457SAndroid Build Coastguard Worker vfpacc0123 = vmulq_f32(vfpacc0123, vscale);
829*4bdc9457SAndroid Build Coastguard Worker vfpacc4567 = vmulq_f32(vfpacc4567, vscale);
830*4bdc9457SAndroid Build Coastguard Worker
831*4bdc9457SAndroid Build Coastguard Worker vacc0123 = vcvtnq_s32_f32(vfpacc0123);
832*4bdc9457SAndroid Build Coastguard Worker vacc4567 = vcvtnq_s32_f32(vfpacc4567);
833*4bdc9457SAndroid Build Coastguard Worker
834*4bdc9457SAndroid Build Coastguard Worker #if XNN_ARCH_ARM64
835*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc01234567 = vqmovn_high_s32(vqmovn_s32(vacc0123), vacc4567);
836*4bdc9457SAndroid Build Coastguard Worker #else
837*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc01234567 = vcombine_s16(vqmovn_s32(vacc0123), vqmovn_s32(vacc4567));
838*4bdc9457SAndroid Build Coastguard Worker #endif
839*4bdc9457SAndroid Build Coastguard Worker vacc01234567 = vqaddq_s16(vacc01234567, voutput_zero_point);
840*4bdc9457SAndroid Build Coastguard Worker
841*4bdc9457SAndroid Build Coastguard Worker uint8x8_t vout01234567 = vqmovun_s16(vacc01234567);
842*4bdc9457SAndroid Build Coastguard Worker vout01234567 = vmax_u8(vout01234567, vget_low_u8(voutput_min));
843*4bdc9457SAndroid Build Coastguard Worker vout01234567 = vmin_u8(vout01234567, vget_low_u8(voutput_max));
844*4bdc9457SAndroid Build Coastguard Worker
845*4bdc9457SAndroid Build Coastguard Worker if XNN_LIKELY(c >= 8) {
846*4bdc9457SAndroid Build Coastguard Worker vst1_u8(output, vout01234567); output += 8;
847*4bdc9457SAndroid Build Coastguard Worker c -= 8;
848*4bdc9457SAndroid Build Coastguard Worker } else {
849*4bdc9457SAndroid Build Coastguard Worker if (c & 4) {
850*4bdc9457SAndroid Build Coastguard Worker vst1_lane_u32((void*) output, vreinterpret_u32_u8(vout01234567), 0); output += 4;
851*4bdc9457SAndroid Build Coastguard Worker vout01234567 = vext_u8(vout01234567, vout01234567, 4);
852*4bdc9457SAndroid Build Coastguard Worker }
853*4bdc9457SAndroid Build Coastguard Worker if (c & 2) {
854*4bdc9457SAndroid Build Coastguard Worker vst1_lane_u16((void*) output, vreinterpret_u16_u8(vout01234567), 0); output += 2;
855*4bdc9457SAndroid Build Coastguard Worker vout01234567 = vext_u8(vout01234567, vout01234567, 2);
856*4bdc9457SAndroid Build Coastguard Worker }
857*4bdc9457SAndroid Build Coastguard Worker if (c & 1) {
858*4bdc9457SAndroid Build Coastguard Worker vst1_lane_u8(output, vout01234567, 0); output += 1;
859*4bdc9457SAndroid Build Coastguard Worker }
860*4bdc9457SAndroid Build Coastguard Worker c = 0;
861*4bdc9457SAndroid Build Coastguard Worker }
862*4bdc9457SAndroid Build Coastguard Worker } while (c != 0);
863*4bdc9457SAndroid Build Coastguard Worker }
864*4bdc9457SAndroid Build Coastguard Worker
865*4bdc9457SAndroid Build Coastguard Worker output = (uint8_t*) ((uintptr_t) output + output_increment);
866*4bdc9457SAndroid Build Coastguard Worker } while (--output_width != 0);
867*4bdc9457SAndroid Build Coastguard Worker }
868