1*4bdc9457SAndroid Build Coastguard Worker // Auto-generated file. Do not edit!
2*4bdc9457SAndroid Build Coastguard Worker // Template: src/qs8-gemm/c2-neon-mull-dup.c.in
3*4bdc9457SAndroid Build Coastguard Worker // Generator: tools/xngen
4*4bdc9457SAndroid Build Coastguard Worker //
5*4bdc9457SAndroid Build Coastguard Worker // Copyright 2021 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/gemm.h>
15*4bdc9457SAndroid Build Coastguard Worker #include <xnnpack/math.h>
16*4bdc9457SAndroid Build Coastguard Worker
xnn_qs8_gemm_minmax_rndnu_ukernel_4x16c2__neon_mlal_ld1r(size_t mr,size_t nc,size_t kc,const int8_t * restrict a,size_t a_stride,const void * restrict w,int8_t * restrict c,size_t cm_stride,size_t cn_stride,const union xnn_qs8_conv_minmax_params params[restrict XNN_MIN_ELEMENTS (1)])17*4bdc9457SAndroid Build Coastguard Worker void xnn_qs8_gemm_minmax_rndnu_ukernel_4x16c2__neon_mlal_ld1r(
18*4bdc9457SAndroid Build Coastguard Worker size_t mr,
19*4bdc9457SAndroid Build Coastguard Worker size_t nc,
20*4bdc9457SAndroid Build Coastguard Worker size_t kc,
21*4bdc9457SAndroid Build Coastguard Worker const int8_t* restrict a,
22*4bdc9457SAndroid Build Coastguard Worker size_t a_stride,
23*4bdc9457SAndroid Build Coastguard Worker const void* restrict w,
24*4bdc9457SAndroid Build Coastguard Worker int8_t* restrict c,
25*4bdc9457SAndroid Build Coastguard Worker size_t cm_stride,
26*4bdc9457SAndroid Build Coastguard Worker size_t cn_stride,
27*4bdc9457SAndroid Build Coastguard Worker const union xnn_qs8_conv_minmax_params params[restrict XNN_MIN_ELEMENTS(1)]) XNN_OOB_READS
28*4bdc9457SAndroid Build Coastguard Worker {
29*4bdc9457SAndroid Build Coastguard Worker assert(mr != 0);
30*4bdc9457SAndroid Build Coastguard Worker assert(mr <= 4);
31*4bdc9457SAndroid Build Coastguard Worker assert(nc != 0);
32*4bdc9457SAndroid Build Coastguard Worker assert(kc != 0);
33*4bdc9457SAndroid Build Coastguard Worker assert(kc % sizeof(int8_t) == 0);
34*4bdc9457SAndroid Build Coastguard Worker assert(a != NULL);
35*4bdc9457SAndroid Build Coastguard Worker assert(w != NULL);
36*4bdc9457SAndroid Build Coastguard Worker assert(c != NULL);
37*4bdc9457SAndroid Build Coastguard Worker
38*4bdc9457SAndroid Build Coastguard Worker kc = round_up_po2(kc, 2 * sizeof(int8_t));
39*4bdc9457SAndroid Build Coastguard Worker const int8_t* a0 = a;
40*4bdc9457SAndroid Build Coastguard Worker int8_t* c0 = c;
41*4bdc9457SAndroid Build Coastguard Worker const int8_t* a1 = (const int8_t*) ((uintptr_t) a0 + a_stride);
42*4bdc9457SAndroid Build Coastguard Worker int8_t* c1 = (int8_t*) ((uintptr_t) c0 + cm_stride);
43*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(mr < 2) {
44*4bdc9457SAndroid Build Coastguard Worker a1 = a0;
45*4bdc9457SAndroid Build Coastguard Worker c1 = c0;
46*4bdc9457SAndroid Build Coastguard Worker }
47*4bdc9457SAndroid Build Coastguard Worker const int8_t* a2 = (const int8_t*) ((uintptr_t) a1 + a_stride);
48*4bdc9457SAndroid Build Coastguard Worker int8_t* c2 = (int8_t*) ((uintptr_t) c1 + cm_stride);
49*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(mr <= 2) {
50*4bdc9457SAndroid Build Coastguard Worker a2 = a1;
51*4bdc9457SAndroid Build Coastguard Worker c2 = c1;
52*4bdc9457SAndroid Build Coastguard Worker }
53*4bdc9457SAndroid Build Coastguard Worker const int8_t* a3 = (const int8_t*) ((uintptr_t) a2 + a_stride);
54*4bdc9457SAndroid Build Coastguard Worker int8_t* c3 = (int8_t*) ((uintptr_t) c2 + cm_stride);
55*4bdc9457SAndroid Build Coastguard Worker if XNN_UNPREDICTABLE(mr != 4) {
56*4bdc9457SAndroid Build Coastguard Worker a3 = a2;
57*4bdc9457SAndroid Build Coastguard Worker c3 = c2;
58*4bdc9457SAndroid Build Coastguard Worker }
59*4bdc9457SAndroid Build Coastguard Worker
60*4bdc9457SAndroid Build Coastguard Worker do {
61*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc0x0123 = vld1q_s32(w); w = (const void*) ((uintptr_t) w + 4 * sizeof(int32_t));
62*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc0x4567 = vld1q_s32(w); w = (const void*) ((uintptr_t) w + 4 * sizeof(int32_t));
63*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc0x89AB = vld1q_s32(w); w = (const void*) ((uintptr_t) w + 4 * sizeof(int32_t));
64*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc0xCDEF = vld1q_s32(w); w = (const void*) ((uintptr_t) w + 4 * sizeof(int32_t));
65*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc1x0123 = vacc0x0123;
66*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc1x4567 = vacc0x4567;
67*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc1x89AB = vacc0x89AB;
68*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc1xCDEF = vacc0xCDEF;
69*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc2x0123 = vacc0x0123;
70*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc2x4567 = vacc0x4567;
71*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc2x89AB = vacc0x89AB;
72*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc2xCDEF = vacc0xCDEF;
73*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc3x0123 = vacc0x0123;
74*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc3x4567 = vacc0x4567;
75*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc3x89AB = vacc0x89AB;
76*4bdc9457SAndroid Build Coastguard Worker int32x4_t vacc3xCDEF = vacc0xCDEF;
77*4bdc9457SAndroid Build Coastguard Worker
78*4bdc9457SAndroid Build Coastguard Worker size_t k = kc;
79*4bdc9457SAndroid Build Coastguard Worker
80*4bdc9457SAndroid Build Coastguard Worker while (k >= 16 * sizeof(int8_t)) {
81*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va00x0 = vld1_dup_s16((const void*)a0);
82*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va01x0 = vld1_dup_s16((const void*)(a0 + 2));
83*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va02x0 = vld1_dup_s16((const void*)(a0 + 4));
84*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va03x0 = vld1_dup_s16((const void*)(a0 + 6)); a0 += 8;
85*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va00x1 = vld1_dup_s16((const void*)a0);
86*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va01x1 = vld1_dup_s16((const void*)(a0 + 2));
87*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va02x1 = vld1_dup_s16((const void*)(a0 + 4));
88*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va03x1 = vld1_dup_s16((const void*)(a0 + 6)); a0 += 8;
89*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va10x0 = vld1_dup_s16((const void*)a1);
90*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va11x0 = vld1_dup_s16((const void*)(a1 + 2));
91*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va12x0 = vld1_dup_s16((const void*)(a1 + 4));
92*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va13x0 = vld1_dup_s16((const void*)(a1 + 6)); a1 += 8;
93*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va10x1 = vld1_dup_s16((const void*)a1);
94*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va11x1 = vld1_dup_s16((const void*)(a1 + 2));
95*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va12x1 = vld1_dup_s16((const void*)(a1 + 4));
96*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va13x1 = vld1_dup_s16((const void*)(a1 + 6)); a1 += 8;
97*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va20x0 = vld1_dup_s16((const void*)a2);
98*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va21x0 = vld1_dup_s16((const void*)(a2 + 2));
99*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va22x0 = vld1_dup_s16((const void*)(a2 + 4));
100*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va23x0 = vld1_dup_s16((const void*)(a2 + 6)); a2 += 8;
101*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va20x1 = vld1_dup_s16((const void*)a2);
102*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va21x1 = vld1_dup_s16((const void*)(a2 + 2));
103*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va22x1 = vld1_dup_s16((const void*)(a2 + 4));
104*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va23x1 = vld1_dup_s16((const void*)(a2 + 6)); a2 += 8;
105*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va30x0 = vld1_dup_s16((const void*)a3);
106*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va31x0 = vld1_dup_s16((const void*)(a3 + 2));
107*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va32x0 = vld1_dup_s16((const void*)(a3 + 4));
108*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va33x0 = vld1_dup_s16((const void*)(a3 + 6)); a3 += 8;
109*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va30x1 = vld1_dup_s16((const void*)a3);
110*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va31x1 = vld1_dup_s16((const void*)(a3 + 2));
111*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va32x1 = vld1_dup_s16((const void*)(a3 + 4));
112*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va33x1 = vld1_dup_s16((const void*)(a3 + 6)); a3 += 8;
113*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c0x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
114*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c0x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
115*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc0x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
116*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc0x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
117*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c1x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
118*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c1x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
119*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc1x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
120*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc1x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
121*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c2x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
122*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c2x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
123*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc2x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
124*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc2x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
125*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c3x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
126*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c3x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
127*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc3x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
128*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc3x0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
129*4bdc9457SAndroid Build Coastguard Worker
130*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c0x0 = vreinterpret_s8_s16(va00x0);
131*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c0x1 = vreinterpret_s8_s16(va00x1);
132*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c0x0 = vreinterpret_s8_s16(va10x0);
133*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c0x1 = vreinterpret_s8_s16(va10x1);
134*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c0x0 = vreinterpret_s8_s16(va20x0);
135*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c0x1 = vreinterpret_s8_s16(va20x1);
136*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c0x0 = vreinterpret_s8_s16(va30x0);
137*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c0x1 = vreinterpret_s8_s16(va30x1);
138*4bdc9457SAndroid Build Coastguard Worker
139*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x0123c0 = vmull_s8(vb0123c0x0, va0c0x0);
140*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x0123c0 = vmull_s8(vb0123c0x0, va1c0x0);
141*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x0123c0 = vmull_s8(vb0123c0x0, va2c0x0);
142*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x0123c0 = vmull_s8(vb0123c0x0, va3c0x0);
143*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c0x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
144*4bdc9457SAndroid Build Coastguard Worker vprod0x0123c0 = vmlal_s8(vprod0x0123c0, vb0123c0x1, va0c0x1);
145*4bdc9457SAndroid Build Coastguard Worker vprod1x0123c0 = vmlal_s8(vprod1x0123c0, vb0123c0x1, va1c0x1);
146*4bdc9457SAndroid Build Coastguard Worker vprod2x0123c0 = vmlal_s8(vprod2x0123c0, vb0123c0x1, va2c0x1);
147*4bdc9457SAndroid Build Coastguard Worker vprod3x0123c0 = vmlal_s8(vprod3x0123c0, vb0123c0x1, va3c0x1);
148*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c0);
149*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c0);
150*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c0);
151*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c0);
152*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x4567c0 = vmull_s8(vb4567c0x0, va0c0x0);
153*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x4567c0 = vmull_s8(vb4567c0x0, va1c0x0);
154*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x4567c0 = vmull_s8(vb4567c0x0, va2c0x0);
155*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x4567c0 = vmull_s8(vb4567c0x0, va3c0x0);
156*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c0x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
157*4bdc9457SAndroid Build Coastguard Worker vprod0x4567c0 = vmlal_s8(vprod0x4567c0, vb4567c0x1, va0c0x1);
158*4bdc9457SAndroid Build Coastguard Worker vprod1x4567c0 = vmlal_s8(vprod1x4567c0, vb4567c0x1, va1c0x1);
159*4bdc9457SAndroid Build Coastguard Worker vprod2x4567c0 = vmlal_s8(vprod2x4567c0, vb4567c0x1, va2c0x1);
160*4bdc9457SAndroid Build Coastguard Worker vprod3x4567c0 = vmlal_s8(vprod3x4567c0, vb4567c0x1, va3c0x1);
161*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c0);
162*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c0);
163*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c0);
164*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c0);
165*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x89ABc0 = vmull_s8(vb89ABc0x0, va0c0x0);
166*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x89ABc0 = vmull_s8(vb89ABc0x0, va1c0x0);
167*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x89ABc0 = vmull_s8(vb89ABc0x0, va2c0x0);
168*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x89ABc0 = vmull_s8(vb89ABc0x0, va3c0x0);
169*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc0x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
170*4bdc9457SAndroid Build Coastguard Worker vprod0x89ABc0 = vmlal_s8(vprod0x89ABc0, vb89ABc0x1, va0c0x1);
171*4bdc9457SAndroid Build Coastguard Worker vprod1x89ABc0 = vmlal_s8(vprod1x89ABc0, vb89ABc0x1, va1c0x1);
172*4bdc9457SAndroid Build Coastguard Worker vprod2x89ABc0 = vmlal_s8(vprod2x89ABc0, vb89ABc0x1, va2c0x1);
173*4bdc9457SAndroid Build Coastguard Worker vprod3x89ABc0 = vmlal_s8(vprod3x89ABc0, vb89ABc0x1, va3c0x1);
174*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc0);
175*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc0);
176*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc0);
177*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc0);
178*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0xCDEFc0 = vmull_s8(vbCDEFc0x0, va0c0x0);
179*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1xCDEFc0 = vmull_s8(vbCDEFc0x0, va1c0x0);
180*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2xCDEFc0 = vmull_s8(vbCDEFc0x0, va2c0x0);
181*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3xCDEFc0 = vmull_s8(vbCDEFc0x0, va3c0x0);
182*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc0x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
183*4bdc9457SAndroid Build Coastguard Worker vprod0xCDEFc0 = vmlal_s8(vprod0xCDEFc0, vbCDEFc0x1, va0c0x1);
184*4bdc9457SAndroid Build Coastguard Worker vprod1xCDEFc0 = vmlal_s8(vprod1xCDEFc0, vbCDEFc0x1, va1c0x1);
185*4bdc9457SAndroid Build Coastguard Worker vprod2xCDEFc0 = vmlal_s8(vprod2xCDEFc0, vbCDEFc0x1, va2c0x1);
186*4bdc9457SAndroid Build Coastguard Worker vprod3xCDEFc0 = vmlal_s8(vprod3xCDEFc0, vbCDEFc0x1, va3c0x1);
187*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc0);
188*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc0);
189*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc0);
190*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc0);
191*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c1x0 = vreinterpret_s8_s16(va01x0);
192*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c1x1 = vreinterpret_s8_s16(va01x1);
193*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c1x0 = vreinterpret_s8_s16(va11x0);
194*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c1x1 = vreinterpret_s8_s16(va11x1);
195*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c1x0 = vreinterpret_s8_s16(va21x0);
196*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c1x1 = vreinterpret_s8_s16(va21x1);
197*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c1x0 = vreinterpret_s8_s16(va31x0);
198*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c1x1 = vreinterpret_s8_s16(va31x1);
199*4bdc9457SAndroid Build Coastguard Worker
200*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x0123c1 = vmull_s8(vb0123c1x0, va0c1x0);
201*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x0123c1 = vmull_s8(vb0123c1x0, va1c1x0);
202*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x0123c1 = vmull_s8(vb0123c1x0, va2c1x0);
203*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x0123c1 = vmull_s8(vb0123c1x0, va3c1x0);
204*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c1x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
205*4bdc9457SAndroid Build Coastguard Worker vprod0x0123c1 = vmlal_s8(vprod0x0123c1, vb0123c1x1, va0c1x1);
206*4bdc9457SAndroid Build Coastguard Worker vprod1x0123c1 = vmlal_s8(vprod1x0123c1, vb0123c1x1, va1c1x1);
207*4bdc9457SAndroid Build Coastguard Worker vprod2x0123c1 = vmlal_s8(vprod2x0123c1, vb0123c1x1, va2c1x1);
208*4bdc9457SAndroid Build Coastguard Worker vprod3x0123c1 = vmlal_s8(vprod3x0123c1, vb0123c1x1, va3c1x1);
209*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c1);
210*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c1);
211*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c1);
212*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c1);
213*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x4567c1 = vmull_s8(vb4567c1x0, va0c1x0);
214*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x4567c1 = vmull_s8(vb4567c1x0, va1c1x0);
215*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x4567c1 = vmull_s8(vb4567c1x0, va2c1x0);
216*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x4567c1 = vmull_s8(vb4567c1x0, va3c1x0);
217*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c1x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
218*4bdc9457SAndroid Build Coastguard Worker vprod0x4567c1 = vmlal_s8(vprod0x4567c1, vb4567c1x1, va0c1x1);
219*4bdc9457SAndroid Build Coastguard Worker vprod1x4567c1 = vmlal_s8(vprod1x4567c1, vb4567c1x1, va1c1x1);
220*4bdc9457SAndroid Build Coastguard Worker vprod2x4567c1 = vmlal_s8(vprod2x4567c1, vb4567c1x1, va2c1x1);
221*4bdc9457SAndroid Build Coastguard Worker vprod3x4567c1 = vmlal_s8(vprod3x4567c1, vb4567c1x1, va3c1x1);
222*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c1);
223*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c1);
224*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c1);
225*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c1);
226*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x89ABc1 = vmull_s8(vb89ABc1x0, va0c1x0);
227*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x89ABc1 = vmull_s8(vb89ABc1x0, va1c1x0);
228*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x89ABc1 = vmull_s8(vb89ABc1x0, va2c1x0);
229*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x89ABc1 = vmull_s8(vb89ABc1x0, va3c1x0);
230*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc1x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
231*4bdc9457SAndroid Build Coastguard Worker vprod0x89ABc1 = vmlal_s8(vprod0x89ABc1, vb89ABc1x1, va0c1x1);
232*4bdc9457SAndroid Build Coastguard Worker vprod1x89ABc1 = vmlal_s8(vprod1x89ABc1, vb89ABc1x1, va1c1x1);
233*4bdc9457SAndroid Build Coastguard Worker vprod2x89ABc1 = vmlal_s8(vprod2x89ABc1, vb89ABc1x1, va2c1x1);
234*4bdc9457SAndroid Build Coastguard Worker vprod3x89ABc1 = vmlal_s8(vprod3x89ABc1, vb89ABc1x1, va3c1x1);
235*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc1);
236*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc1);
237*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc1);
238*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc1);
239*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0xCDEFc1 = vmull_s8(vbCDEFc1x0, va0c1x0);
240*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1xCDEFc1 = vmull_s8(vbCDEFc1x0, va1c1x0);
241*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2xCDEFc1 = vmull_s8(vbCDEFc1x0, va2c1x0);
242*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3xCDEFc1 = vmull_s8(vbCDEFc1x0, va3c1x0);
243*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc1x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
244*4bdc9457SAndroid Build Coastguard Worker vprod0xCDEFc1 = vmlal_s8(vprod0xCDEFc1, vbCDEFc1x1, va0c1x1);
245*4bdc9457SAndroid Build Coastguard Worker vprod1xCDEFc1 = vmlal_s8(vprod1xCDEFc1, vbCDEFc1x1, va1c1x1);
246*4bdc9457SAndroid Build Coastguard Worker vprod2xCDEFc1 = vmlal_s8(vprod2xCDEFc1, vbCDEFc1x1, va2c1x1);
247*4bdc9457SAndroid Build Coastguard Worker vprod3xCDEFc1 = vmlal_s8(vprod3xCDEFc1, vbCDEFc1x1, va3c1x1);
248*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc1);
249*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc1);
250*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc1);
251*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc1);
252*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c2x0 = vreinterpret_s8_s16(va02x0);
253*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c2x1 = vreinterpret_s8_s16(va02x1);
254*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c2x0 = vreinterpret_s8_s16(va12x0);
255*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c2x1 = vreinterpret_s8_s16(va12x1);
256*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c2x0 = vreinterpret_s8_s16(va22x0);
257*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c2x1 = vreinterpret_s8_s16(va22x1);
258*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c2x0 = vreinterpret_s8_s16(va32x0);
259*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c2x1 = vreinterpret_s8_s16(va32x1);
260*4bdc9457SAndroid Build Coastguard Worker
261*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x0123c2 = vmull_s8(vb0123c2x0, va0c2x0);
262*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x0123c2 = vmull_s8(vb0123c2x0, va1c2x0);
263*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x0123c2 = vmull_s8(vb0123c2x0, va2c2x0);
264*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x0123c2 = vmull_s8(vb0123c2x0, va3c2x0);
265*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c2x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
266*4bdc9457SAndroid Build Coastguard Worker vprod0x0123c2 = vmlal_s8(vprod0x0123c2, vb0123c2x1, va0c2x1);
267*4bdc9457SAndroid Build Coastguard Worker vprod1x0123c2 = vmlal_s8(vprod1x0123c2, vb0123c2x1, va1c2x1);
268*4bdc9457SAndroid Build Coastguard Worker vprod2x0123c2 = vmlal_s8(vprod2x0123c2, vb0123c2x1, va2c2x1);
269*4bdc9457SAndroid Build Coastguard Worker vprod3x0123c2 = vmlal_s8(vprod3x0123c2, vb0123c2x1, va3c2x1);
270*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c2);
271*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c2);
272*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c2);
273*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c2);
274*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x4567c2 = vmull_s8(vb4567c2x0, va0c2x0);
275*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x4567c2 = vmull_s8(vb4567c2x0, va1c2x0);
276*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x4567c2 = vmull_s8(vb4567c2x0, va2c2x0);
277*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x4567c2 = vmull_s8(vb4567c2x0, va3c2x0);
278*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c2x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
279*4bdc9457SAndroid Build Coastguard Worker vprod0x4567c2 = vmlal_s8(vprod0x4567c2, vb4567c2x1, va0c2x1);
280*4bdc9457SAndroid Build Coastguard Worker vprod1x4567c2 = vmlal_s8(vprod1x4567c2, vb4567c2x1, va1c2x1);
281*4bdc9457SAndroid Build Coastguard Worker vprod2x4567c2 = vmlal_s8(vprod2x4567c2, vb4567c2x1, va2c2x1);
282*4bdc9457SAndroid Build Coastguard Worker vprod3x4567c2 = vmlal_s8(vprod3x4567c2, vb4567c2x1, va3c2x1);
283*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c2);
284*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c2);
285*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c2);
286*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c2);
287*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x89ABc2 = vmull_s8(vb89ABc2x0, va0c2x0);
288*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x89ABc2 = vmull_s8(vb89ABc2x0, va1c2x0);
289*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x89ABc2 = vmull_s8(vb89ABc2x0, va2c2x0);
290*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x89ABc2 = vmull_s8(vb89ABc2x0, va3c2x0);
291*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc2x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
292*4bdc9457SAndroid Build Coastguard Worker vprod0x89ABc2 = vmlal_s8(vprod0x89ABc2, vb89ABc2x1, va0c2x1);
293*4bdc9457SAndroid Build Coastguard Worker vprod1x89ABc2 = vmlal_s8(vprod1x89ABc2, vb89ABc2x1, va1c2x1);
294*4bdc9457SAndroid Build Coastguard Worker vprod2x89ABc2 = vmlal_s8(vprod2x89ABc2, vb89ABc2x1, va2c2x1);
295*4bdc9457SAndroid Build Coastguard Worker vprod3x89ABc2 = vmlal_s8(vprod3x89ABc2, vb89ABc2x1, va3c2x1);
296*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc2);
297*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc2);
298*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc2);
299*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc2);
300*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0xCDEFc2 = vmull_s8(vbCDEFc2x0, va0c2x0);
301*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1xCDEFc2 = vmull_s8(vbCDEFc2x0, va1c2x0);
302*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2xCDEFc2 = vmull_s8(vbCDEFc2x0, va2c2x0);
303*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3xCDEFc2 = vmull_s8(vbCDEFc2x0, va3c2x0);
304*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc2x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
305*4bdc9457SAndroid Build Coastguard Worker vprod0xCDEFc2 = vmlal_s8(vprod0xCDEFc2, vbCDEFc2x1, va0c2x1);
306*4bdc9457SAndroid Build Coastguard Worker vprod1xCDEFc2 = vmlal_s8(vprod1xCDEFc2, vbCDEFc2x1, va1c2x1);
307*4bdc9457SAndroid Build Coastguard Worker vprod2xCDEFc2 = vmlal_s8(vprod2xCDEFc2, vbCDEFc2x1, va2c2x1);
308*4bdc9457SAndroid Build Coastguard Worker vprod3xCDEFc2 = vmlal_s8(vprod3xCDEFc2, vbCDEFc2x1, va3c2x1);
309*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc2);
310*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc2);
311*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc2);
312*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc2);
313*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c3x0 = vreinterpret_s8_s16(va03x0);
314*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c3x1 = vreinterpret_s8_s16(va03x1);
315*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c3x0 = vreinterpret_s8_s16(va13x0);
316*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c3x1 = vreinterpret_s8_s16(va13x1);
317*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c3x0 = vreinterpret_s8_s16(va23x0);
318*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c3x1 = vreinterpret_s8_s16(va23x1);
319*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c3x0 = vreinterpret_s8_s16(va33x0);
320*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c3x1 = vreinterpret_s8_s16(va33x1);
321*4bdc9457SAndroid Build Coastguard Worker
322*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x0123c3 = vmull_s8(vb0123c3x0, va0c3x0);
323*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x0123c3 = vmull_s8(vb0123c3x0, va1c3x0);
324*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x0123c3 = vmull_s8(vb0123c3x0, va2c3x0);
325*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x0123c3 = vmull_s8(vb0123c3x0, va3c3x0);
326*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c3x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
327*4bdc9457SAndroid Build Coastguard Worker vprod0x0123c3 = vmlal_s8(vprod0x0123c3, vb0123c3x1, va0c3x1);
328*4bdc9457SAndroid Build Coastguard Worker vprod1x0123c3 = vmlal_s8(vprod1x0123c3, vb0123c3x1, va1c3x1);
329*4bdc9457SAndroid Build Coastguard Worker vprod2x0123c3 = vmlal_s8(vprod2x0123c3, vb0123c3x1, va2c3x1);
330*4bdc9457SAndroid Build Coastguard Worker vprod3x0123c3 = vmlal_s8(vprod3x0123c3, vb0123c3x1, va3c3x1);
331*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c3);
332*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c3);
333*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c3);
334*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c3);
335*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x4567c3 = vmull_s8(vb4567c3x0, va0c3x0);
336*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x4567c3 = vmull_s8(vb4567c3x0, va1c3x0);
337*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x4567c3 = vmull_s8(vb4567c3x0, va2c3x0);
338*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x4567c3 = vmull_s8(vb4567c3x0, va3c3x0);
339*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c3x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
340*4bdc9457SAndroid Build Coastguard Worker vprod0x4567c3 = vmlal_s8(vprod0x4567c3, vb4567c3x1, va0c3x1);
341*4bdc9457SAndroid Build Coastguard Worker vprod1x4567c3 = vmlal_s8(vprod1x4567c3, vb4567c3x1, va1c3x1);
342*4bdc9457SAndroid Build Coastguard Worker vprod2x4567c3 = vmlal_s8(vprod2x4567c3, vb4567c3x1, va2c3x1);
343*4bdc9457SAndroid Build Coastguard Worker vprod3x4567c3 = vmlal_s8(vprod3x4567c3, vb4567c3x1, va3c3x1);
344*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c3);
345*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c3);
346*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c3);
347*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c3);
348*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0x89ABc3 = vmull_s8(vb89ABc3x0, va0c3x0);
349*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1x89ABc3 = vmull_s8(vb89ABc3x0, va1c3x0);
350*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2x89ABc3 = vmull_s8(vb89ABc3x0, va2c3x0);
351*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3x89ABc3 = vmull_s8(vb89ABc3x0, va3c3x0);
352*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc3x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
353*4bdc9457SAndroid Build Coastguard Worker vprod0x89ABc3 = vmlal_s8(vprod0x89ABc3, vb89ABc3x1, va0c3x1);
354*4bdc9457SAndroid Build Coastguard Worker vprod1x89ABc3 = vmlal_s8(vprod1x89ABc3, vb89ABc3x1, va1c3x1);
355*4bdc9457SAndroid Build Coastguard Worker vprod2x89ABc3 = vmlal_s8(vprod2x89ABc3, vb89ABc3x1, va2c3x1);
356*4bdc9457SAndroid Build Coastguard Worker vprod3x89ABc3 = vmlal_s8(vprod3x89ABc3, vb89ABc3x1, va3c3x1);
357*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc3);
358*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc3);
359*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc3);
360*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc3);
361*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod0xCDEFc3 = vmull_s8(vbCDEFc3x0, va0c3x0);
362*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod1xCDEFc3 = vmull_s8(vbCDEFc3x0, va1c3x0);
363*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod2xCDEFc3 = vmull_s8(vbCDEFc3x0, va2c3x0);
364*4bdc9457SAndroid Build Coastguard Worker int16x8_t vprod3xCDEFc3 = vmull_s8(vbCDEFc3x0, va3c3x0);
365*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc3x1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
366*4bdc9457SAndroid Build Coastguard Worker vprod0xCDEFc3 = vmlal_s8(vprod0xCDEFc3, vbCDEFc3x1, va0c3x1);
367*4bdc9457SAndroid Build Coastguard Worker vprod1xCDEFc3 = vmlal_s8(vprod1xCDEFc3, vbCDEFc3x1, va1c3x1);
368*4bdc9457SAndroid Build Coastguard Worker vprod2xCDEFc3 = vmlal_s8(vprod2xCDEFc3, vbCDEFc3x1, va2c3x1);
369*4bdc9457SAndroid Build Coastguard Worker vprod3xCDEFc3 = vmlal_s8(vprod3xCDEFc3, vbCDEFc3x1, va3c3x1);
370*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc3);
371*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc3);
372*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc3);
373*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc3);
374*4bdc9457SAndroid Build Coastguard Worker
375*4bdc9457SAndroid Build Coastguard Worker k -= 16 * sizeof(int8_t);
376*4bdc9457SAndroid Build Coastguard Worker }
377*4bdc9457SAndroid Build Coastguard Worker
378*4bdc9457SAndroid Build Coastguard Worker if (k >= 8 * sizeof(int8_t)) {
379*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va00 = vld1_dup_s16((const void*)a0);
380*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va01 = vld1_dup_s16((const void*)(a0 + 2));
381*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va02 = vld1_dup_s16((const void*)(a0 + 4));
382*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va03 = vld1_dup_s16((const void*)(a0 + 6)); a0 += 8;
383*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va10 = vld1_dup_s16((const void*)a1);
384*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va11 = vld1_dup_s16((const void*)(a1 + 2));
385*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va12 = vld1_dup_s16((const void*)(a1 + 4));
386*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va13 = vld1_dup_s16((const void*)(a1 + 6)); a1 += 8;
387*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va20 = vld1_dup_s16((const void*)a2);
388*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va21 = vld1_dup_s16((const void*)(a2 + 2));
389*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va22 = vld1_dup_s16((const void*)(a2 + 4));
390*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va23 = vld1_dup_s16((const void*)(a2 + 6)); a2 += 8;
391*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va30 = vld1_dup_s16((const void*)a3);
392*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va31 = vld1_dup_s16((const void*)(a3 + 2));
393*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va32 = vld1_dup_s16((const void*)(a3 + 4));
394*4bdc9457SAndroid Build Coastguard Worker const int16x4_t va33 = vld1_dup_s16((const void*)(a3 + 6)); a3 += 8;
395*4bdc9457SAndroid Build Coastguard Worker
396*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
397*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
398*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
399*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
400*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
401*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
402*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
403*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
404*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c2 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
405*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c2 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
406*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc2 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
407*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc2 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
408*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c3 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
409*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c3 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
410*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc3 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
411*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc3 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
412*4bdc9457SAndroid Build Coastguard Worker
413*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c0 = vreinterpret_s8_s16(va00);
414*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c0 = vreinterpret_s8_s16(va10);
415*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c0 = vreinterpret_s8_s16(va20);
416*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c0 = vreinterpret_s8_s16(va30);
417*4bdc9457SAndroid Build Coastguard Worker
418*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x0123c0 = vmull_s8(vb0123c0, va0c0);
419*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x0123c0 = vmull_s8(vb0123c0, va1c0);
420*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x0123c0 = vmull_s8(vb0123c0, va2c0);
421*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x0123c0 = vmull_s8(vb0123c0, va3c0);
422*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c0);
423*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c0);
424*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c0);
425*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c0);
426*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x4567c0 = vmull_s8(vb4567c0, va0c0);
427*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x4567c0 = vmull_s8(vb4567c0, va1c0);
428*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x4567c0 = vmull_s8(vb4567c0, va2c0);
429*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x4567c0 = vmull_s8(vb4567c0, va3c0);
430*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c0);
431*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c0);
432*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c0);
433*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c0);
434*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x89ABc0 = vmull_s8(vb89ABc0, va0c0);
435*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x89ABc0 = vmull_s8(vb89ABc0, va1c0);
436*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x89ABc0 = vmull_s8(vb89ABc0, va2c0);
437*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x89ABc0 = vmull_s8(vb89ABc0, va3c0);
438*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc0);
439*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc0);
440*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc0);
441*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc0);
442*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0xCDEFc0 = vmull_s8(vbCDEFc0, va0c0);
443*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1xCDEFc0 = vmull_s8(vbCDEFc0, va1c0);
444*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2xCDEFc0 = vmull_s8(vbCDEFc0, va2c0);
445*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3xCDEFc0 = vmull_s8(vbCDEFc0, va3c0);
446*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc0);
447*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc0);
448*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc0);
449*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc0);
450*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c1 = vreinterpret_s8_s16(va01);
451*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c1 = vreinterpret_s8_s16(va11);
452*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c1 = vreinterpret_s8_s16(va21);
453*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c1 = vreinterpret_s8_s16(va31);
454*4bdc9457SAndroid Build Coastguard Worker
455*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x0123c1 = vmull_s8(vb0123c1, va0c1);
456*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x0123c1 = vmull_s8(vb0123c1, va1c1);
457*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x0123c1 = vmull_s8(vb0123c1, va2c1);
458*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x0123c1 = vmull_s8(vb0123c1, va3c1);
459*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c1);
460*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c1);
461*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c1);
462*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c1);
463*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x4567c1 = vmull_s8(vb4567c1, va0c1);
464*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x4567c1 = vmull_s8(vb4567c1, va1c1);
465*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x4567c1 = vmull_s8(vb4567c1, va2c1);
466*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x4567c1 = vmull_s8(vb4567c1, va3c1);
467*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c1);
468*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c1);
469*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c1);
470*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c1);
471*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x89ABc1 = vmull_s8(vb89ABc1, va0c1);
472*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x89ABc1 = vmull_s8(vb89ABc1, va1c1);
473*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x89ABc1 = vmull_s8(vb89ABc1, va2c1);
474*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x89ABc1 = vmull_s8(vb89ABc1, va3c1);
475*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc1);
476*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc1);
477*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc1);
478*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc1);
479*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0xCDEFc1 = vmull_s8(vbCDEFc1, va0c1);
480*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1xCDEFc1 = vmull_s8(vbCDEFc1, va1c1);
481*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2xCDEFc1 = vmull_s8(vbCDEFc1, va2c1);
482*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3xCDEFc1 = vmull_s8(vbCDEFc1, va3c1);
483*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc1);
484*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc1);
485*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc1);
486*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc1);
487*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c2 = vreinterpret_s8_s16(va02);
488*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c2 = vreinterpret_s8_s16(va12);
489*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c2 = vreinterpret_s8_s16(va22);
490*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c2 = vreinterpret_s8_s16(va32);
491*4bdc9457SAndroid Build Coastguard Worker
492*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x0123c2 = vmull_s8(vb0123c2, va0c2);
493*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x0123c2 = vmull_s8(vb0123c2, va1c2);
494*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x0123c2 = vmull_s8(vb0123c2, va2c2);
495*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x0123c2 = vmull_s8(vb0123c2, va3c2);
496*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c2);
497*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c2);
498*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c2);
499*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c2);
500*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x4567c2 = vmull_s8(vb4567c2, va0c2);
501*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x4567c2 = vmull_s8(vb4567c2, va1c2);
502*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x4567c2 = vmull_s8(vb4567c2, va2c2);
503*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x4567c2 = vmull_s8(vb4567c2, va3c2);
504*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c2);
505*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c2);
506*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c2);
507*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c2);
508*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x89ABc2 = vmull_s8(vb89ABc2, va0c2);
509*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x89ABc2 = vmull_s8(vb89ABc2, va1c2);
510*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x89ABc2 = vmull_s8(vb89ABc2, va2c2);
511*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x89ABc2 = vmull_s8(vb89ABc2, va3c2);
512*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc2);
513*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc2);
514*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc2);
515*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc2);
516*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0xCDEFc2 = vmull_s8(vbCDEFc2, va0c2);
517*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1xCDEFc2 = vmull_s8(vbCDEFc2, va1c2);
518*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2xCDEFc2 = vmull_s8(vbCDEFc2, va2c2);
519*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3xCDEFc2 = vmull_s8(vbCDEFc2, va3c2);
520*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc2);
521*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc2);
522*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc2);
523*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc2);
524*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c3 = vreinterpret_s8_s16(va03);
525*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c3 = vreinterpret_s8_s16(va13);
526*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c3 = vreinterpret_s8_s16(va23);
527*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c3 = vreinterpret_s8_s16(va33);
528*4bdc9457SAndroid Build Coastguard Worker
529*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x0123c3 = vmull_s8(vb0123c3, va0c3);
530*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x0123c3 = vmull_s8(vb0123c3, va1c3);
531*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x0123c3 = vmull_s8(vb0123c3, va2c3);
532*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x0123c3 = vmull_s8(vb0123c3, va3c3);
533*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c3);
534*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c3);
535*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c3);
536*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c3);
537*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x4567c3 = vmull_s8(vb4567c3, va0c3);
538*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x4567c3 = vmull_s8(vb4567c3, va1c3);
539*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x4567c3 = vmull_s8(vb4567c3, va2c3);
540*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x4567c3 = vmull_s8(vb4567c3, va3c3);
541*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c3);
542*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c3);
543*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c3);
544*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c3);
545*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x89ABc3 = vmull_s8(vb89ABc3, va0c3);
546*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x89ABc3 = vmull_s8(vb89ABc3, va1c3);
547*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x89ABc3 = vmull_s8(vb89ABc3, va2c3);
548*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x89ABc3 = vmull_s8(vb89ABc3, va3c3);
549*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc3);
550*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc3);
551*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc3);
552*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc3);
553*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0xCDEFc3 = vmull_s8(vbCDEFc3, va0c3);
554*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1xCDEFc3 = vmull_s8(vbCDEFc3, va1c3);
555*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2xCDEFc3 = vmull_s8(vbCDEFc3, va2c3);
556*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3xCDEFc3 = vmull_s8(vbCDEFc3, va3c3);
557*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc3);
558*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc3);
559*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc3);
560*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc3);
561*4bdc9457SAndroid Build Coastguard Worker
562*4bdc9457SAndroid Build Coastguard Worker k -= 8 * sizeof(int8_t);
563*4bdc9457SAndroid Build Coastguard Worker }
564*4bdc9457SAndroid Build Coastguard Worker
565*4bdc9457SAndroid Build Coastguard Worker if XNN_UNLIKELY(k != 0) {
566*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0 = vld1_s8(a0); a0 = (const int8_t*) ((uintptr_t) a0 + k);
567*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1 = vld1_s8(a1); a1 = (const int8_t*) ((uintptr_t) a1 + k);
568*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2 = vld1_s8(a2); a2 = (const int8_t*) ((uintptr_t) a2 + k);
569*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3 = vld1_s8(a3); a3 = (const int8_t*) ((uintptr_t) a3 + k);
570*4bdc9457SAndroid Build Coastguard Worker
571*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
572*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
573*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
574*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc0 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
575*4bdc9457SAndroid Build Coastguard Worker
576*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c0 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va0), 0));
577*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x0123c0 = vmull_s8(vb0123c0, va0c0);
578*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c0);
579*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x4567c0 = vmull_s8(vb4567c0, va0c0);
580*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c0);
581*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x89ABc0 = vmull_s8(vb89ABc0, va0c0);
582*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc0);
583*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0xCDEFc0 = vmull_s8(vbCDEFc0, va0c0);
584*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc0);
585*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c0 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va1), 0));
586*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x0123c0 = vmull_s8(vb0123c0, va1c0);
587*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c0);
588*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x4567c0 = vmull_s8(vb4567c0, va1c0);
589*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c0);
590*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x89ABc0 = vmull_s8(vb89ABc0, va1c0);
591*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc0);
592*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1xCDEFc0 = vmull_s8(vbCDEFc0, va1c0);
593*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc0);
594*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c0 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va2), 0));
595*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x0123c0 = vmull_s8(vb0123c0, va2c0);
596*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c0);
597*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x4567c0 = vmull_s8(vb4567c0, va2c0);
598*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c0);
599*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x89ABc0 = vmull_s8(vb89ABc0, va2c0);
600*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc0);
601*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2xCDEFc0 = vmull_s8(vbCDEFc0, va2c0);
602*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc0);
603*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c0 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va3), 0));
604*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x0123c0 = vmull_s8(vb0123c0, va3c0);
605*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c0);
606*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x4567c0 = vmull_s8(vb4567c0, va3c0);
607*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c0);
608*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x89ABc0 = vmull_s8(vb89ABc0, va3c0);
609*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc0);
610*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3xCDEFc0 = vmull_s8(vbCDEFc0, va3c0);
611*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc0);
612*4bdc9457SAndroid Build Coastguard Worker
613*4bdc9457SAndroid Build Coastguard Worker if (k > 2 * sizeof(int8_t)) {
614*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
615*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
616*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
617*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc1 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
618*4bdc9457SAndroid Build Coastguard Worker
619*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c1 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va0), 1));
620*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x0123c1 = vmull_s8(vb0123c1, va0c1);
621*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c1);
622*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x4567c1 = vmull_s8(vb4567c1, va0c1);
623*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c1);
624*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x89ABc1 = vmull_s8(vb89ABc1, va0c1);
625*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc1);
626*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0xCDEFc1 = vmull_s8(vbCDEFc1, va0c1);
627*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc1);
628*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c1 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va1), 1));
629*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x0123c1 = vmull_s8(vb0123c1, va1c1);
630*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c1);
631*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x4567c1 = vmull_s8(vb4567c1, va1c1);
632*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c1);
633*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x89ABc1 = vmull_s8(vb89ABc1, va1c1);
634*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc1);
635*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1xCDEFc1 = vmull_s8(vbCDEFc1, va1c1);
636*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc1);
637*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c1 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va2), 1));
638*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x0123c1 = vmull_s8(vb0123c1, va2c1);
639*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c1);
640*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x4567c1 = vmull_s8(vb4567c1, va2c1);
641*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c1);
642*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x89ABc1 = vmull_s8(vb89ABc1, va2c1);
643*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc1);
644*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2xCDEFc1 = vmull_s8(vbCDEFc1, va2c1);
645*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc1);
646*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c1 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va3), 1));
647*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x0123c1 = vmull_s8(vb0123c1, va3c1);
648*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c1);
649*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x4567c1 = vmull_s8(vb4567c1, va3c1);
650*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c1);
651*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x89ABc1 = vmull_s8(vb89ABc1, va3c1);
652*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc1);
653*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3xCDEFc1 = vmull_s8(vbCDEFc1, va3c1);
654*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc1);
655*4bdc9457SAndroid Build Coastguard Worker
656*4bdc9457SAndroid Build Coastguard Worker if (k > 4 * sizeof(int8_t)) {
657*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb0123c2 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
658*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb4567c2 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
659*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vb89ABc2 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
660*4bdc9457SAndroid Build Coastguard Worker const int8x8_t vbCDEFc2 = vld1_s8(w); w = (const void*) ((uintptr_t) w + 8 * sizeof(int8_t));
661*4bdc9457SAndroid Build Coastguard Worker
662*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va0c2 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va0), 2));
663*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x0123c2 = vmull_s8(vb0123c2, va0c2);
664*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vpadalq_s16(vacc0x0123, vprod0x0123c2);
665*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x4567c2 = vmull_s8(vb4567c2, va0c2);
666*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vpadalq_s16(vacc0x4567, vprod0x4567c2);
667*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0x89ABc2 = vmull_s8(vb89ABc2, va0c2);
668*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vpadalq_s16(vacc0x89AB, vprod0x89ABc2);
669*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod0xCDEFc2 = vmull_s8(vbCDEFc2, va0c2);
670*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vpadalq_s16(vacc0xCDEF, vprod0xCDEFc2);
671*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va1c2 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va1), 2));
672*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x0123c2 = vmull_s8(vb0123c2, va1c2);
673*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vpadalq_s16(vacc1x0123, vprod1x0123c2);
674*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x4567c2 = vmull_s8(vb4567c2, va1c2);
675*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vpadalq_s16(vacc1x4567, vprod1x4567c2);
676*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1x89ABc2 = vmull_s8(vb89ABc2, va1c2);
677*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vpadalq_s16(vacc1x89AB, vprod1x89ABc2);
678*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod1xCDEFc2 = vmull_s8(vbCDEFc2, va1c2);
679*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vpadalq_s16(vacc1xCDEF, vprod1xCDEFc2);
680*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va2c2 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va2), 2));
681*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x0123c2 = vmull_s8(vb0123c2, va2c2);
682*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vpadalq_s16(vacc2x0123, vprod2x0123c2);
683*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x4567c2 = vmull_s8(vb4567c2, va2c2);
684*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vpadalq_s16(vacc2x4567, vprod2x4567c2);
685*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2x89ABc2 = vmull_s8(vb89ABc2, va2c2);
686*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vpadalq_s16(vacc2x89AB, vprod2x89ABc2);
687*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod2xCDEFc2 = vmull_s8(vbCDEFc2, va2c2);
688*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vpadalq_s16(vacc2xCDEF, vprod2xCDEFc2);
689*4bdc9457SAndroid Build Coastguard Worker const int8x8_t va3c2 = vreinterpret_s8_s16(vdup_lane_s16(vreinterpret_s16_s8(va3), 2));
690*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x0123c2 = vmull_s8(vb0123c2, va3c2);
691*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vpadalq_s16(vacc3x0123, vprod3x0123c2);
692*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x4567c2 = vmull_s8(vb4567c2, va3c2);
693*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vpadalq_s16(vacc3x4567, vprod3x4567c2);
694*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3x89ABc2 = vmull_s8(vb89ABc2, va3c2);
695*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vpadalq_s16(vacc3x89AB, vprod3x89ABc2);
696*4bdc9457SAndroid Build Coastguard Worker const int16x8_t vprod3xCDEFc2 = vmull_s8(vbCDEFc2, va3c2);
697*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vpadalq_s16(vacc3xCDEF, vprod3xCDEFc2);
698*4bdc9457SAndroid Build Coastguard Worker }
699*4bdc9457SAndroid Build Coastguard Worker }
700*4bdc9457SAndroid Build Coastguard Worker }
701*4bdc9457SAndroid Build Coastguard Worker
702*4bdc9457SAndroid Build Coastguard Worker const int32x4_t vright_pre_shift = vld1q_dup_s32(¶ms->rndnu_neon.right_pre_shift);
703*4bdc9457SAndroid Build Coastguard Worker const int32x4_t vmultiplier = vld1q_dup_s32(¶ms->rndnu_neon.multiplier);
704*4bdc9457SAndroid Build Coastguard Worker const int32x4_t vright_post_shift = vld1q_dup_s32(¶ms->rndnu_neon.right_post_shift);
705*4bdc9457SAndroid Build Coastguard Worker
706*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vqshlq_s32(vacc0x0123, vright_pre_shift);
707*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vqshlq_s32(vacc0x4567, vright_pre_shift);
708*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vqshlq_s32(vacc0x89AB, vright_pre_shift);
709*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vqshlq_s32(vacc0xCDEF, vright_pre_shift);
710*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vqshlq_s32(vacc1x0123, vright_pre_shift);
711*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vqshlq_s32(vacc1x4567, vright_pre_shift);
712*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vqshlq_s32(vacc1x89AB, vright_pre_shift);
713*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vqshlq_s32(vacc1xCDEF, vright_pre_shift);
714*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vqshlq_s32(vacc2x0123, vright_pre_shift);
715*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vqshlq_s32(vacc2x4567, vright_pre_shift);
716*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vqshlq_s32(vacc2x89AB, vright_pre_shift);
717*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vqshlq_s32(vacc2xCDEF, vright_pre_shift);
718*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vqshlq_s32(vacc3x0123, vright_pre_shift);
719*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vqshlq_s32(vacc3x4567, vright_pre_shift);
720*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vqshlq_s32(vacc3x89AB, vright_pre_shift);
721*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vqshlq_s32(vacc3xCDEF, vright_pre_shift);
722*4bdc9457SAndroid Build Coastguard Worker
723*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vqdmulhq_s32(vacc0x0123, vmultiplier);
724*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vqdmulhq_s32(vacc0x4567, vmultiplier);
725*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vqdmulhq_s32(vacc0x89AB, vmultiplier);
726*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vqdmulhq_s32(vacc0xCDEF, vmultiplier);
727*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vqdmulhq_s32(vacc1x0123, vmultiplier);
728*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vqdmulhq_s32(vacc1x4567, vmultiplier);
729*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vqdmulhq_s32(vacc1x89AB, vmultiplier);
730*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vqdmulhq_s32(vacc1xCDEF, vmultiplier);
731*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vqdmulhq_s32(vacc2x0123, vmultiplier);
732*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vqdmulhq_s32(vacc2x4567, vmultiplier);
733*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vqdmulhq_s32(vacc2x89AB, vmultiplier);
734*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vqdmulhq_s32(vacc2xCDEF, vmultiplier);
735*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vqdmulhq_s32(vacc3x0123, vmultiplier);
736*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vqdmulhq_s32(vacc3x4567, vmultiplier);
737*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vqdmulhq_s32(vacc3x89AB, vmultiplier);
738*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vqdmulhq_s32(vacc3xCDEF, vmultiplier);
739*4bdc9457SAndroid Build Coastguard Worker
740*4bdc9457SAndroid Build Coastguard Worker vacc0x0123 = vrshlq_s32(vacc0x0123, vright_post_shift);
741*4bdc9457SAndroid Build Coastguard Worker vacc0x4567 = vrshlq_s32(vacc0x4567, vright_post_shift);
742*4bdc9457SAndroid Build Coastguard Worker vacc0x89AB = vrshlq_s32(vacc0x89AB, vright_post_shift);
743*4bdc9457SAndroid Build Coastguard Worker vacc0xCDEF = vrshlq_s32(vacc0xCDEF, vright_post_shift);
744*4bdc9457SAndroid Build Coastguard Worker vacc1x0123 = vrshlq_s32(vacc1x0123, vright_post_shift);
745*4bdc9457SAndroid Build Coastguard Worker vacc1x4567 = vrshlq_s32(vacc1x4567, vright_post_shift);
746*4bdc9457SAndroid Build Coastguard Worker vacc1x89AB = vrshlq_s32(vacc1x89AB, vright_post_shift);
747*4bdc9457SAndroid Build Coastguard Worker vacc1xCDEF = vrshlq_s32(vacc1xCDEF, vright_post_shift);
748*4bdc9457SAndroid Build Coastguard Worker vacc2x0123 = vrshlq_s32(vacc2x0123, vright_post_shift);
749*4bdc9457SAndroid Build Coastguard Worker vacc2x4567 = vrshlq_s32(vacc2x4567, vright_post_shift);
750*4bdc9457SAndroid Build Coastguard Worker vacc2x89AB = vrshlq_s32(vacc2x89AB, vright_post_shift);
751*4bdc9457SAndroid Build Coastguard Worker vacc2xCDEF = vrshlq_s32(vacc2xCDEF, vright_post_shift);
752*4bdc9457SAndroid Build Coastguard Worker vacc3x0123 = vrshlq_s32(vacc3x0123, vright_post_shift);
753*4bdc9457SAndroid Build Coastguard Worker vacc3x4567 = vrshlq_s32(vacc3x4567, vright_post_shift);
754*4bdc9457SAndroid Build Coastguard Worker vacc3x89AB = vrshlq_s32(vacc3x89AB, vright_post_shift);
755*4bdc9457SAndroid Build Coastguard Worker vacc3xCDEF = vrshlq_s32(vacc3xCDEF, vright_post_shift);
756*4bdc9457SAndroid Build Coastguard Worker
757*4bdc9457SAndroid Build Coastguard Worker const int16x8_t voutput_zero_point = vld1q_dup_s16(¶ms->rndnu_neon.output_zero_point);
758*4bdc9457SAndroid Build Coastguard Worker #if XNN_ARCH_ARM64
759*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc0x01234567 = vqmovn_high_s32(vqmovn_s32(vacc0x0123), vacc0x4567);
760*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc0x89ABCDEF = vqmovn_high_s32(vqmovn_s32(vacc0x89AB), vacc0xCDEF);
761*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc1x01234567 = vqmovn_high_s32(vqmovn_s32(vacc1x0123), vacc1x4567);
762*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc1x89ABCDEF = vqmovn_high_s32(vqmovn_s32(vacc1x89AB), vacc1xCDEF);
763*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc2x01234567 = vqmovn_high_s32(vqmovn_s32(vacc2x0123), vacc2x4567);
764*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc2x89ABCDEF = vqmovn_high_s32(vqmovn_s32(vacc2x89AB), vacc2xCDEF);
765*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc3x01234567 = vqmovn_high_s32(vqmovn_s32(vacc3x0123), vacc3x4567);
766*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc3x89ABCDEF = vqmovn_high_s32(vqmovn_s32(vacc3x89AB), vacc3xCDEF);
767*4bdc9457SAndroid Build Coastguard Worker
768*4bdc9457SAndroid Build Coastguard Worker vacc0x01234567 = vqaddq_s16(vacc0x01234567, voutput_zero_point);
769*4bdc9457SAndroid Build Coastguard Worker vacc0x89ABCDEF = vqaddq_s16(vacc0x89ABCDEF, voutput_zero_point);
770*4bdc9457SAndroid Build Coastguard Worker vacc1x01234567 = vqaddq_s16(vacc1x01234567, voutput_zero_point);
771*4bdc9457SAndroid Build Coastguard Worker vacc1x89ABCDEF = vqaddq_s16(vacc1x89ABCDEF, voutput_zero_point);
772*4bdc9457SAndroid Build Coastguard Worker vacc2x01234567 = vqaddq_s16(vacc2x01234567, voutput_zero_point);
773*4bdc9457SAndroid Build Coastguard Worker vacc2x89ABCDEF = vqaddq_s16(vacc2x89ABCDEF, voutput_zero_point);
774*4bdc9457SAndroid Build Coastguard Worker vacc3x01234567 = vqaddq_s16(vacc3x01234567, voutput_zero_point);
775*4bdc9457SAndroid Build Coastguard Worker vacc3x89ABCDEF = vqaddq_s16(vacc3x89ABCDEF, voutput_zero_point);
776*4bdc9457SAndroid Build Coastguard Worker
777*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout0x0123456789ABCDEF = vqmovn_high_s16(vqmovn_s16(vacc0x01234567), vacc0x89ABCDEF);
778*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout1x0123456789ABCDEF = vqmovn_high_s16(vqmovn_s16(vacc1x01234567), vacc1x89ABCDEF);
779*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout2x0123456789ABCDEF = vqmovn_high_s16(vqmovn_s16(vacc2x01234567), vacc2x89ABCDEF);
780*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout3x0123456789ABCDEF = vqmovn_high_s16(vqmovn_s16(vacc3x01234567), vacc3x89ABCDEF);
781*4bdc9457SAndroid Build Coastguard Worker #else
782*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc0x01234567 = vcombine_s16(vqmovn_s32(vacc0x0123), vqmovn_s32(vacc0x4567));
783*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc0x89ABCDEF = vcombine_s16(vqmovn_s32(vacc0x89AB), vqmovn_s32(vacc0xCDEF));
784*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc1x01234567 = vcombine_s16(vqmovn_s32(vacc1x0123), vqmovn_s32(vacc1x4567));
785*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc1x89ABCDEF = vcombine_s16(vqmovn_s32(vacc1x89AB), vqmovn_s32(vacc1xCDEF));
786*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc2x01234567 = vcombine_s16(vqmovn_s32(vacc2x0123), vqmovn_s32(vacc2x4567));
787*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc2x89ABCDEF = vcombine_s16(vqmovn_s32(vacc2x89AB), vqmovn_s32(vacc2xCDEF));
788*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc3x01234567 = vcombine_s16(vqmovn_s32(vacc3x0123), vqmovn_s32(vacc3x4567));
789*4bdc9457SAndroid Build Coastguard Worker int16x8_t vacc3x89ABCDEF = vcombine_s16(vqmovn_s32(vacc3x89AB), vqmovn_s32(vacc3xCDEF));
790*4bdc9457SAndroid Build Coastguard Worker
791*4bdc9457SAndroid Build Coastguard Worker vacc0x01234567 = vqaddq_s16(vacc0x01234567, voutput_zero_point);
792*4bdc9457SAndroid Build Coastguard Worker vacc0x89ABCDEF = vqaddq_s16(vacc0x89ABCDEF, voutput_zero_point);
793*4bdc9457SAndroid Build Coastguard Worker vacc1x01234567 = vqaddq_s16(vacc1x01234567, voutput_zero_point);
794*4bdc9457SAndroid Build Coastguard Worker vacc1x89ABCDEF = vqaddq_s16(vacc1x89ABCDEF, voutput_zero_point);
795*4bdc9457SAndroid Build Coastguard Worker vacc2x01234567 = vqaddq_s16(vacc2x01234567, voutput_zero_point);
796*4bdc9457SAndroid Build Coastguard Worker vacc2x89ABCDEF = vqaddq_s16(vacc2x89ABCDEF, voutput_zero_point);
797*4bdc9457SAndroid Build Coastguard Worker vacc3x01234567 = vqaddq_s16(vacc3x01234567, voutput_zero_point);
798*4bdc9457SAndroid Build Coastguard Worker vacc3x89ABCDEF = vqaddq_s16(vacc3x89ABCDEF, voutput_zero_point);
799*4bdc9457SAndroid Build Coastguard Worker
800*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout0x0123456789ABCDEF = vcombine_s8(vqmovn_s16(vacc0x01234567), vqmovn_s16(vacc0x89ABCDEF));
801*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout1x0123456789ABCDEF = vcombine_s8(vqmovn_s16(vacc1x01234567), vqmovn_s16(vacc1x89ABCDEF));
802*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout2x0123456789ABCDEF = vcombine_s8(vqmovn_s16(vacc2x01234567), vqmovn_s16(vacc2x89ABCDEF));
803*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout3x0123456789ABCDEF = vcombine_s8(vqmovn_s16(vacc3x01234567), vqmovn_s16(vacc3x89ABCDEF));
804*4bdc9457SAndroid Build Coastguard Worker #endif
805*4bdc9457SAndroid Build Coastguard Worker
806*4bdc9457SAndroid Build Coastguard Worker const int8x16_t voutput_min = vld1q_dup_s8(¶ms->rndnu_neon.output_min);
807*4bdc9457SAndroid Build Coastguard Worker vout0x0123456789ABCDEF = vmaxq_s8(vout0x0123456789ABCDEF, voutput_min);
808*4bdc9457SAndroid Build Coastguard Worker vout1x0123456789ABCDEF = vmaxq_s8(vout1x0123456789ABCDEF, voutput_min);
809*4bdc9457SAndroid Build Coastguard Worker vout2x0123456789ABCDEF = vmaxq_s8(vout2x0123456789ABCDEF, voutput_min);
810*4bdc9457SAndroid Build Coastguard Worker vout3x0123456789ABCDEF = vmaxq_s8(vout3x0123456789ABCDEF, voutput_min);
811*4bdc9457SAndroid Build Coastguard Worker
812*4bdc9457SAndroid Build Coastguard Worker const int8x16_t voutput_max = vld1q_dup_s8(¶ms->rndnu_neon.output_max);
813*4bdc9457SAndroid Build Coastguard Worker vout0x0123456789ABCDEF = vminq_s8(vout0x0123456789ABCDEF, voutput_max);
814*4bdc9457SAndroid Build Coastguard Worker vout1x0123456789ABCDEF = vminq_s8(vout1x0123456789ABCDEF, voutput_max);
815*4bdc9457SAndroid Build Coastguard Worker vout2x0123456789ABCDEF = vminq_s8(vout2x0123456789ABCDEF, voutput_max);
816*4bdc9457SAndroid Build Coastguard Worker vout3x0123456789ABCDEF = vminq_s8(vout3x0123456789ABCDEF, voutput_max);
817*4bdc9457SAndroid Build Coastguard Worker
818*4bdc9457SAndroid Build Coastguard Worker if (nc >= 16) {
819*4bdc9457SAndroid Build Coastguard Worker vst1q_s8(c0 + 0, vout0x0123456789ABCDEF);
820*4bdc9457SAndroid Build Coastguard Worker vst1q_s8(c1 + 0, vout1x0123456789ABCDEF);
821*4bdc9457SAndroid Build Coastguard Worker vst1q_s8(c2 + 0, vout2x0123456789ABCDEF);
822*4bdc9457SAndroid Build Coastguard Worker vst1q_s8(c3 + 0, vout3x0123456789ABCDEF);
823*4bdc9457SAndroid Build Coastguard Worker
824*4bdc9457SAndroid Build Coastguard Worker c0 = (int8_t*) ((uintptr_t) c0 + cn_stride);
825*4bdc9457SAndroid Build Coastguard Worker c1 = (int8_t*) ((uintptr_t) c1 + cn_stride);
826*4bdc9457SAndroid Build Coastguard Worker c2 = (int8_t*) ((uintptr_t) c2 + cn_stride);
827*4bdc9457SAndroid Build Coastguard Worker c3 = (int8_t*) ((uintptr_t) c3 + cn_stride);
828*4bdc9457SAndroid Build Coastguard Worker
829*4bdc9457SAndroid Build Coastguard Worker a0 = (const int8_t*) ((uintptr_t) a0 - kc);
830*4bdc9457SAndroid Build Coastguard Worker a1 = (const int8_t*) ((uintptr_t) a1 - kc);
831*4bdc9457SAndroid Build Coastguard Worker a2 = (const int8_t*) ((uintptr_t) a2 - kc);
832*4bdc9457SAndroid Build Coastguard Worker a3 = (const int8_t*) ((uintptr_t) a3 - kc);
833*4bdc9457SAndroid Build Coastguard Worker
834*4bdc9457SAndroid Build Coastguard Worker nc -= 16;
835*4bdc9457SAndroid Build Coastguard Worker } else {
836*4bdc9457SAndroid Build Coastguard Worker // Final case where not all of the 16 columns fit in the destination.
837*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout0x01234567_1x01234567 = vcombine_s8(vget_low_s8(vout0x0123456789ABCDEF), vget_low_s8(vout1x0123456789ABCDEF));
838*4bdc9457SAndroid Build Coastguard Worker int8x16_t vout2x01234567_3x01234567 = vcombine_s8(vget_low_s8(vout2x0123456789ABCDEF), vget_low_s8(vout3x0123456789ABCDEF));
839*4bdc9457SAndroid Build Coastguard Worker if (nc & 8) {
840*4bdc9457SAndroid Build Coastguard Worker vst1_s8(c0, vget_low_s8(vout0x01234567_1x01234567)); c0 += 8;
841*4bdc9457SAndroid Build Coastguard Worker vst1_s8(c1, vget_high_s8(vout0x01234567_1x01234567)); c1 += 8;
842*4bdc9457SAndroid Build Coastguard Worker vst1_s8(c2, vget_low_s8(vout2x01234567_3x01234567)); c2 += 8;
843*4bdc9457SAndroid Build Coastguard Worker vst1_s8(c3, vget_high_s8(vout2x01234567_3x01234567)); c3 += 8;
844*4bdc9457SAndroid Build Coastguard Worker vout0x01234567_1x01234567 = vcombine_s8(vget_high_s8(vout0x0123456789ABCDEF), vget_high_s8(vout1x0123456789ABCDEF));
845*4bdc9457SAndroid Build Coastguard Worker vout2x01234567_3x01234567 = vcombine_s8(vget_high_s8(vout2x0123456789ABCDEF), vget_high_s8(vout3x0123456789ABCDEF));
846*4bdc9457SAndroid Build Coastguard Worker }
847*4bdc9457SAndroid Build Coastguard Worker if (nc & 4) {
848*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_u32((void*) c0, vreinterpretq_u32_s8(vout0x01234567_1x01234567), 0); c0 += 4;
849*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_u32((void*) c1, vreinterpretq_u32_s8(vout0x01234567_1x01234567), 2); c1 += 4;
850*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_u32((void*) c2, vreinterpretq_u32_s8(vout2x01234567_3x01234567), 0); c2 += 4;
851*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_u32((void*) c3, vreinterpretq_u32_s8(vout2x01234567_3x01234567), 2); c3 += 4;
852*4bdc9457SAndroid Build Coastguard Worker vout0x01234567_1x01234567 = vextq_s8(vout0x01234567_1x01234567, vout0x01234567_1x01234567, 4);
853*4bdc9457SAndroid Build Coastguard Worker vout2x01234567_3x01234567 = vextq_s8(vout2x01234567_3x01234567, vout2x01234567_3x01234567, 4);
854*4bdc9457SAndroid Build Coastguard Worker }
855*4bdc9457SAndroid Build Coastguard Worker if (nc & 2) {
856*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_u16((void*) c0, vreinterpretq_u16_s8(vout0x01234567_1x01234567), 0); c0 += 2;
857*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_u16((void*) c1, vreinterpretq_u16_s8(vout0x01234567_1x01234567), 4); c1 += 2;
858*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_u16((void*) c2, vreinterpretq_u16_s8(vout2x01234567_3x01234567), 0); c2 += 2;
859*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_u16((void*) c3, vreinterpretq_u16_s8(vout2x01234567_3x01234567), 4); c3 += 2;
860*4bdc9457SAndroid Build Coastguard Worker vout0x01234567_1x01234567 = vextq_s8(vout0x01234567_1x01234567, vout0x01234567_1x01234567, 2);
861*4bdc9457SAndroid Build Coastguard Worker vout2x01234567_3x01234567 = vextq_s8(vout2x01234567_3x01234567, vout2x01234567_3x01234567, 2);
862*4bdc9457SAndroid Build Coastguard Worker }
863*4bdc9457SAndroid Build Coastguard Worker if (nc & 1) {
864*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_s8(c0, vout0x01234567_1x01234567, 0);
865*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_s8(c1, vout0x01234567_1x01234567, 8);
866*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_s8(c2, vout2x01234567_3x01234567, 0);
867*4bdc9457SAndroid Build Coastguard Worker vst1q_lane_s8(c3, vout2x01234567_3x01234567, 8);
868*4bdc9457SAndroid Build Coastguard Worker }
869*4bdc9457SAndroid Build Coastguard Worker
870*4bdc9457SAndroid Build Coastguard Worker nc = 0;
871*4bdc9457SAndroid Build Coastguard Worker }
872*4bdc9457SAndroid Build Coastguard Worker } while (nc != 0);
873*4bdc9457SAndroid Build Coastguard Worker }
874