#include "src/aarch64/matrix_mul/int16/strategy.h"
#include "src/aarch64/matrix_mul/asm/common.h"
#include "src/aarch64/matrix_mul/int16/kernel_12x8x1.h"
#include "src/arm_common/simd_macro/marm_neon.h"
#include "src/common/utils.h"
using namespace megdnn;
using namespace aarch64;
using namespace aarch64::matmul;
MEGDNN_REG_GEMM_STRATEGY_IMPL(gemm_s16_12x8x1);
void gemm_s16_12x8x1::pack_A(
dt_int16* outptr, const dt_int16* inptr, int ldin, int y0, int ymax, int k0,
int kmax, bool transpose) const {
if (transpose) {
matmul_12x8x1::gemm_s16_12x8x1_transpose_pack_A_n(
outptr, inptr, ldin, y0, ymax, k0, kmax);
} else {
matmul_12x8x1::gemm_s16_12x8x1_pack_A_n(
outptr, inptr, ldin, y0, ymax, k0, kmax);
}
}
void gemm_s16_12x8x1::pack_B(
dt_int16* out, const dt_int16* in, int ldin, int x0, int xmax, int k0, int kmax,
bool transpose) const {
if (transpose) {
matmul_12x8x1::gemm_s16_12x8x1_transpose_pack_B_n(
out, in, ldin, x0, xmax, k0, kmax);
} else {
matmul_12x8x1::gemm_s16_12x8x1_pack_B_n(out, in, ldin, x0, xmax, k0, kmax);
}
}
void gemm_s16_12x8x1::kern(
const dt_int16* packA, const dt_int16* packB, size_t M, size_t N, size_t K,
dt_int32* C, size_t LDC, bool is_first_k, const dt_int32*, dt_int32*) const {
megdnn_assert(
A_dtype.enumv() == B_dtype.enumv() &&
(A_dtype.enumv() == DTypeEnum::Int16 &&
C_dtype.enumv() == DTypeEnum::Int32),
"A: %s B: %s C: %s", A_dtype.name(), B_dtype.name(), C_dtype.name());
MEGDNN_MARK_USED_VAR(A_dtype);
MEGDNN_MARK_USED_VAR(B_dtype);
MEGDNN_MARK_USED_VAR(C_dtype);
constexpr size_t A_INTERLEAVE = 12;
constexpr size_t B_INTERLEAVE = 8;
const int K12 = K * 12;
const int K8 = K * 8;
const int K4 = K * 4;
size_t m = 0;
for (; m + A_INTERLEAVE - 1 < M; m += A_INTERLEAVE) {
int32_t* output = C + (m * LDC);
size_t n = 0;
const dt_int16* cur_packB = packB;
for (; n + B_INTERLEAVE - 1 < N; n += B_INTERLEAVE) {
matmul_12x8x1::kern_12x8(packA, cur_packB, K, output, LDC, is_first_k);
output += B_INTERLEAVE;
cur_packB += K8;
}
for (; n < N; n += 4) {
matmul_12x8x1::kern_12x4(
packA, cur_packB, K, output, LDC, is_first_k,
std::min<size_t>(N - n, 4));
output += 4;
cur_packB += K4;
}
packA += K12;
}
for (; m + 7 < M; m += 8) {
int32_t* output = C + (m * LDC);
const dt_int16* cur_packB = packB;
size_t n = 0;
for (; n + B_INTERLEAVE - 1 < N; n += B_INTERLEAVE) {
matmul_12x8x1::kern_8x8(packA, cur_packB, K, output, LDC, is_first_k);
output += B_INTERLEAVE;
cur_packB += K8;
}
for (; n < N; n += 4) {
matmul_12x8x1::kern_8x4(
packA, cur_packB, K, output, LDC, is_first_k,
std::min<size_t>(N - n, 4));
output += 4;
cur_packB += K4;
}
packA += K8;
}
for (; m < M; m += 4) {
int32_t* output = C + (m * LDC);
const dt_int16* cur_packB = packB;
size_t n = 0;
for (; n + B_INTERLEAVE - 1 < N; n += B_INTERLEAVE) {
matmul_12x8x1::kern_4x8(
packA, cur_packB, K, output, LDC, is_first_k,
std::min<size_t>(M - m, 4));
output += B_INTERLEAVE;
cur_packB += K8;
}
for (; n < N; n += 4) {
matmul_12x8x1::kern_4x4(
packA, cur_packB, K, output, LDC, is_first_k,
std::min<size_t>(M - m, 4), std::min<size_t>(N - n, 4));
output += 4;
cur_packB += K4;
}
packA += K4;
}
}