mirror of https://github.com/alibaba/MNN.git
66 lines
2.6 KiB
C++
66 lines
2.6 KiB
C++
//
|
|
// SPDX-FileCopyrightText: Copyright 2024 Arm Limited and/or its affiliates <open-source-office@arm.com>
|
|
//
|
|
// SPDX-License-Identifier: Apache-2.0
|
|
//
|
|
|
|
#include <arm_neon.h>
|
|
#include <assert.h>
|
|
#include <cfloat>
|
|
#include <stdint.h>
|
|
#include <string.h>
|
|
#include <vector>
|
|
|
|
#include "kai_lhs_quant_pack_qai8dxp_f32.h"
|
|
#include "kai_rhs_pack_nxk_qsi4cxp_qs4cxs1s0.h"
|
|
#include "kai_rhs_pack_nxk_qsi4cxps1s0_qsu4cxs1s0_neon.h"
|
|
#include "kai_matmul_clamp_f32_qai8dxp1x8_qsi4cxp4x8_1x4x32_neon_dotprod.h"
|
|
#include "kai_matmul_clamp_f32_qai8dxp4x8_qsi4cxp4x8_8x4x32_neon_i8mm.h"
|
|
#include "kai_matmul_clamp_f32_qai8dxp1vlx8_qsi4cxp4vlx8_1vlx4vl_sme2_mopa.h"
|
|
#include "kai_matmul_clamp_f32_qai8dxp1x4_qsi4cxp4vlx4_1x4vl_sme2_sdot.h"
|
|
|
|
#include "kai_lhs_quant_pack_qsi8d32pscalef32_f16_neon.h"
|
|
#include "kai_lhs_quant_pack_qsi8d32pscalef32_f32_neon.h"
|
|
#include "kai_rhs_pack_nxk_qai4c32p_qau4c32s0s1_f32_f32_f32_neon.h"
|
|
#include "kai_matmul_clamp_f16_qsi8d32p1x8_qai4c32p4x8_1x4_neon_dotprod.h"
|
|
#include "kai_matmul_clamp_f16_qsi8d32p4x8_qai4c32p4x8_8x4_neon_i8mm.h"
|
|
#include "kai_matmul_clamp_f32_qsi8d32p1x8_qai4c32p4x8_1x4_neon_dotprod.h"
|
|
#include "kai_matmul_clamp_f32_qsi8d32p4x8_qai4c32p4x8_8x4_neon_i8mm.h"
|
|
|
|
#include "kai_rhs_pack_nxk_f32p2vlx1biasf32_f32_f32_sme.h"
|
|
#include "kai_lhs_pack_f32p2vlx1_f32_sme.h"
|
|
#include "kai_matmul_clamp_f32_f32p2vlx1_f32p2vlx1biasf32_sme2_mopa.h"
|
|
#include "kai_matmul_clamp_f32_f32_f32p16vlx1b_1x16vl_sme2_mla.h"
|
|
#include "kai_matmul_clamp_f32_f32_f32p2vlx1b_1x16vl_sme2_mla.h"
|
|
|
|
#include "kai_lhs_pack_x16p2vlx2_x16_sme.h"
|
|
#include "kai_rhs_pack_nxk_x16p2vlx2b_x16_x16_sme.h"
|
|
#include "kai_matmul_clamp_f16_f16p2vlx2_f16p2vlx2_2vlx2vl_sme2_mopa.h"
|
|
#include "kai_matmul_clamp_f16_f16_f16p2vlx2b_1x16vl_sme2_dot.h"
|
|
|
|
#include "kai_common.h"
|
|
|
|
namespace MNN {
|
|
class KleidiAIUtil {
|
|
public:
|
|
struct rhsPackParamCommon {
|
|
int8_t mLhsZeroPoint = 1;
|
|
uint8_t mRhsZeroPoint = 8;
|
|
};
|
|
|
|
/// Rhs pack functions for matmul_clamp_f32_qai8dxp_qsi4cxp.
|
|
static void packQsi4cxps16s0Qs4cxs0s1(
|
|
size_t num_groups, size_t n, size_t k, size_t nr, size_t kr, size_t sr,
|
|
const uint8_t* rhs, const float* bias, const float* scale,
|
|
void* rhs_packed,
|
|
size_t extra_bytes,
|
|
const struct KleidiAIUtil::rhsPackParamCommon* paramsCommon);
|
|
|
|
static void packQsi4cxps1s0Qsu4cxs0s1(
|
|
size_t num_groups, size_t n, size_t k, size_t nr, size_t kr, size_t sr,
|
|
const uint8_t* rhs, const float* bias, const float* scale,
|
|
void* rhs_packed,
|
|
size_t extra_bytes,
|
|
const struct KleidiAIUtil::rhsPackParamCommon* paramsCommon);
|
|
};
|
|
} |