1*4bdc9457SAndroid Build Coastguard Worker // Copyright 2019 Google LLC
2*4bdc9457SAndroid Build Coastguard Worker //
3*4bdc9457SAndroid Build Coastguard Worker // This source code is licensed under the BSD-style license found in the
4*4bdc9457SAndroid Build Coastguard Worker // LICENSE file in the root directory of this source tree.
5*4bdc9457SAndroid Build Coastguard Worker
6*4bdc9457SAndroid Build Coastguard Worker #include <assert.h>
7*4bdc9457SAndroid Build Coastguard Worker
8*4bdc9457SAndroid Build Coastguard Worker #include <arm_neon.h>
9*4bdc9457SAndroid Build Coastguard Worker
10*4bdc9457SAndroid Build Coastguard Worker #include <xnnpack/packx.h>
11*4bdc9457SAndroid Build Coastguard Worker
12*4bdc9457SAndroid Build Coastguard Worker
xnn_x32_packx_ukernel_4x__neon_st4(size_t m,size_t k,const uint32_t * restrict x,size_t x_stride,uint32_t * restrict y)13*4bdc9457SAndroid Build Coastguard Worker void xnn_x32_packx_ukernel_4x__neon_st4(
14*4bdc9457SAndroid Build Coastguard Worker size_t m,
15*4bdc9457SAndroid Build Coastguard Worker size_t k,
16*4bdc9457SAndroid Build Coastguard Worker const uint32_t* restrict x,
17*4bdc9457SAndroid Build Coastguard Worker size_t x_stride,
18*4bdc9457SAndroid Build Coastguard Worker uint32_t* restrict y)
19*4bdc9457SAndroid Build Coastguard Worker {
20*4bdc9457SAndroid Build Coastguard Worker assert(m != 0);
21*4bdc9457SAndroid Build Coastguard Worker assert(k != 0);
22*4bdc9457SAndroid Build Coastguard Worker
23*4bdc9457SAndroid Build Coastguard Worker const uint32_t* x0 = x;
24*4bdc9457SAndroid Build Coastguard Worker const uint32_t* x1 = (const uint32_t*) ((uintptr_t) x0 + x_stride);
25*4bdc9457SAndroid Build Coastguard Worker if (m < 2) {
26*4bdc9457SAndroid Build Coastguard Worker x1 = x0;
27*4bdc9457SAndroid Build Coastguard Worker }
28*4bdc9457SAndroid Build Coastguard Worker const uint32_t* x2 = (const uint32_t*) ((uintptr_t) x1 + x_stride);
29*4bdc9457SAndroid Build Coastguard Worker if (m <= 2) {
30*4bdc9457SAndroid Build Coastguard Worker x2 = x1;
31*4bdc9457SAndroid Build Coastguard Worker }
32*4bdc9457SAndroid Build Coastguard Worker const uint32_t* x3 = (const uint32_t*) ((uintptr_t) x2 + x_stride);
33*4bdc9457SAndroid Build Coastguard Worker if (m != 4) {
34*4bdc9457SAndroid Build Coastguard Worker x3 = x2;
35*4bdc9457SAndroid Build Coastguard Worker }
36*4bdc9457SAndroid Build Coastguard Worker
37*4bdc9457SAndroid Build Coastguard Worker for (; k >= 4; k -= 4) {
38*4bdc9457SAndroid Build Coastguard Worker const uint32x4_t vx0 = vld1q_u32(x0); x0 += 4;
39*4bdc9457SAndroid Build Coastguard Worker const uint32x4_t vx1 = vld1q_u32(x1); x1 += 4;
40*4bdc9457SAndroid Build Coastguard Worker const uint32x4_t vx2 = vld1q_u32(x2); x2 += 4;
41*4bdc9457SAndroid Build Coastguard Worker const uint32x4_t vx3 = vld1q_u32(x3); x3 += 4;
42*4bdc9457SAndroid Build Coastguard Worker
43*4bdc9457SAndroid Build Coastguard Worker const uint32x4x4_t vy = { vx0, vx1, vx2, vx3 };
44*4bdc9457SAndroid Build Coastguard Worker vst4q_u32(y, vy); y += 16;
45*4bdc9457SAndroid Build Coastguard Worker }
46*4bdc9457SAndroid Build Coastguard Worker if XNN_UNLIKELY(k != 0) {
47*4bdc9457SAndroid Build Coastguard Worker do {
48*4bdc9457SAndroid Build Coastguard Worker const uint32x2_t vx00 = vld1_dup_u32(x0); x0 += 1;
49*4bdc9457SAndroid Build Coastguard Worker const uint32x2_t vx22 = vld1_dup_u32(x2); x2 += 1;
50*4bdc9457SAndroid Build Coastguard Worker const uint32x2_t vx01 = vld1_lane_u32(x1, vx00, 1); x1 += 1;
51*4bdc9457SAndroid Build Coastguard Worker const uint32x2_t vx23 = vld1_lane_u32(x3, vx22, 1); x3 += 1;
52*4bdc9457SAndroid Build Coastguard Worker const uint32x4_t vy = vcombine_u32(vx01, vx23);
53*4bdc9457SAndroid Build Coastguard Worker vst1q_u32(y, vy); y += 4;
54*4bdc9457SAndroid Build Coastguard Worker } while (--k != 0);
55*4bdc9457SAndroid Build Coastguard Worker }
56*4bdc9457SAndroid Build Coastguard Worker }
57