diff --git a/cmake/libs/libfaiss.cmake b/cmake/libs/libfaiss.cmake index 1e99fc6ac..63898ab6e 100644 --- a/cmake/libs/libfaiss.cmake +++ b/cmake/libs/libfaiss.cmake @@ -47,9 +47,18 @@ if(__X86_64) endif() if(__AARCH64) - set(UTILS_SRC src/simd/hook.cc src/simd/distances_ref.cc - src/simd/distances_neon.cc) - add_library(knowhere_utils STATIC ${UTILS_SRC}) + set(UTILS_SRC src/simd/hook.cc src/simd/distances_ref.cc) + + # Add separate utils for NEON and SVE + add_library(utils_neon OBJECT src/simd/distances_neon.cc) + add_library(utils_sve OBJECT src/simd/distances_sve.cc) + + target_compile_options(utils_neon PRIVATE -march=armv8-a+simd) + target_compile_options(utils_sve PRIVATE -march=armv8-a+sve) + + add_library( + knowhere_utils STATIC + ${UTILS_SRC} $ $) target_link_libraries(knowhere_utils PUBLIC glog::glog) endif() diff --git a/src/simd/distances_sve.cc b/src/simd/distances_sve.cc new file mode 100644 index 000000000..edc03da2a --- /dev/null +++ b/src/simd/distances_sve.cc @@ -0,0 +1,185 @@ +// Copyright (C) 2019-2023 Zilliz. All rights reserved. +// +// Licensed under the Apache License, Version 2.0 (the "License"); you may not use this file except in compliance +// with the License. You may obtain a copy of the License at +// +// http://www.apache.org/licenses/LICENSE-2.0 +// +// Unless required by applicable law or agreed to in writing, software distributed under the License +// is distributed on an "AS IS" BASIS, WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express +// or implied. See the License for the specific language governing permissions and limitations under the License. + +#include "distances_sve.h" + +#include + +#include + +#include "faiss/impl/platform_macros.h" +#pragma GCC optimize("O3,fast-math,inline") +#if defined(__ARM_FEATURE_SVE) +namespace faiss { + +float +fvec_L2sqr_sve(const float* x, const float* y, size_t d) { + svfloat32_t sum = svdup_f32(0.0f); + size_t i = 0; + + svbool_t pg = svptrue_b32(); + + while (i < d) { + if (d - i < svcntw()) + pg = svwhilelt_b32(i, d); + + svfloat32_t a = svld1_f32(pg, x + i); + svfloat32_t b = svld1_f32(pg, y + i); + svfloat32_t diff = svsub_f32_m(pg, a, b); + sum = svmla_f32_m(pg, sum, diff, diff); + i += svcntw(); + } + + return svaddv_f32(svptrue_b32(), sum); +} + +float +fvec_L1_sve(const float* x, const float* y, size_t d) { + svfloat32_t sum = svdup_f32(0.0f); + size_t i = 0; + + svbool_t pg = svptrue_b32(); + + while (i < d) { + if (d - i < svcntw()) + pg = svwhilelt_b32(i, d); + + svfloat32_t a = svld1_f32(pg, x + i); + svfloat32_t b = svld1_f32(pg, y + i); + svfloat32_t diff = svabs_f32_x(pg, svsub_f32_m(pg, a, b)); + sum = svadd_f32_m(pg, sum, diff); + i += svcntw(); + } + + return svaddv_f32(svptrue_b32(), sum); +} + +float +fvec_Linf_sve(const float* x, const float* y, size_t d) { + svfloat32_t max_val = svdup_f32(0.0f); + size_t i = 0; + + svbool_t pg = svptrue_b32(); + + while (i < d) { + if (d - i < svcntw()) + pg = svwhilelt_b32(i, d); + + svfloat32_t a = svld1_f32(pg, x + i); + svfloat32_t b = svld1_f32(pg, y + i); + svfloat32_t diff = svabs_f32_x(pg, svsub_f32_m(pg, a, b)); + max_val = svmax_f32_m(pg, max_val, diff); + i += svcntw(); + } + + return svmaxv_f32(svptrue_b32(), max_val); +} + +float +fvec_norm_L2sqr_sve(const float* x, size_t d) { + svfloat32_t sum = svdup_f32(0.0f); + size_t i = 0; + + svbool_t pg = svptrue_b32(); + + while (i < d) { + if (d - i < svcntw()) + pg = svwhilelt_b32(i, d); + + svfloat32_t a = svld1_f32(pg, x + i); + sum = svmla_f32_m(pg, sum, a, a); + i += svcntw(); + } + + return svaddv_f32(svptrue_b32(), sum); +} + +void +fvec_madd_sve(size_t n, const float* a, float bf, const float* b, float* c) { + size_t i = 0; + svfloat32_t bf_vec = svdup_f32(bf); + + svbool_t pg = svptrue_b32(); + + while (i < n) { + if (n - i < svcntw()) + pg = svwhilelt_b32(i, n); + + svfloat32_t a_vec = svld1_f32(pg, a + i); + svfloat32_t b_vec = svld1_f32(pg, b + i); + svfloat32_t c_vec = svmla_f32_m(pg, a_vec, b_vec, bf_vec); + svst1_f32(pg, c + i, c_vec); + i += svcntw(); + } +} + +int +fvec_madd_and_argmin_sve(size_t n, const float* a, float bf, const float* b, float* c) { + size_t i = 0; + svfloat32_t min_val = svdup_f32(INFINITY); + svuint32_t min_idx = svdup_u32(0); + svuint32_t idx_base = svindex_u32(0, 1); + + svfloat32_t bf_vec = svdup_f32(bf); + svbool_t pg = svptrue_b32(); + + while (i < n) { + if (n - i < svcntw()) + pg = svwhilelt_b32(i, n); + + svuint32_t idx = svadd_u32_z(pg, idx_base, svdup_u32(i)); + svfloat32_t a_vec = svld1_f32(pg, a + i); + svfloat32_t b_vec = svld1_f32(pg, b + i); + svfloat32_t c_vec = svmla_f32_m(pg, a_vec, b_vec, bf_vec); + svst1_f32(pg, c + i, c_vec); + + svbool_t cmp = svcmplt(pg, c_vec, min_val); + min_val = svsel_f32(cmp, c_vec, min_val); + min_idx = svsel_u32(cmp, idx, min_idx); + + i += svcntw(); + } + + float min_value = svminv_f32(svptrue_b32(), min_val); + svbool_t pg_min = svcmpeq(svptrue_b32(), min_val, svdup_f32(min_value)); + uint32_t min_index = svlastb_u32(pg_min, min_idx); + + return static_cast(min_index); +} + +void +fvec_L2sqr_batch_4_sve(const float* x, const float* y0, const float* y1, const float* y2, const float* y3, + const size_t d, float& dis0, float& dis1, float& dis2, float& dis3) { + float d0 = 0; + float d1 = 0; + float d2 = 0; + float d3 = 0; + + for (size_t i = 0; i < d; ++i) { + const float q0 = x[i] - y0[i]; + const float q1 = x[i] - y1[i]; + const float q2 = x[i] - y2[i]; + const float q3 = x[i] - y3[i]; + d0 += q0 * q0; + d1 += q1 * q1; + d2 += q2 * q2; + d3 += q3 * q3; + } + + dis0 = d0; + dis1 = d1; + dis2 = d2; + dis3 = d3; +} + +} // namespace faiss + +#endif diff --git a/src/simd/distances_sve.h b/src/simd/distances_sve.h new file mode 100644 index 000000000..4ec403e79 --- /dev/null +++ b/src/simd/distances_sve.h @@ -0,0 +1,45 @@ +// Copyright (C) 2019-2023 Zilliz. All rights reserved. +// +// Licensed under the Apache License, Version 2.0 (the "License"); you may not use this file except in compliance +// with the License. You may obtain a copy of the License at +// +// http://www.apache.org/licenses/LICENSE-2.0 +// +// Unless required by applicable law or agreed to in writing, software distributed under the License +// is distributed on an "AS IS" BASIS, WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express +// or implied. See the License for the specific language governing permissions and limitations under the License. + +#include + +#include +#include +#if defined(__ARM_FEATURE_SVE) +namespace faiss { + +float +fvec_L2sqr_sve(const float* x, const float* y, size_t d); + +float +fvec_L1_sve(const float* x, const float* y, size_t d); + +float +fvec_Linf_sve(const float* x, const float* y, size_t d); + +float +fvec_norm_L2sqr_sve(const float* x, size_t d); + +void +fvec_madd_sve(size_t n, const float* a, float bf, const float* b, float* c); + +int +fvec_madd_and_argmin_sve(size_t n, const float* a, float bf, const float* b, float* c); + +int32_t +ivec_L2sqr_sve(const int8_t* x, const int8_t* y, size_t d); + +void +fvec_L2sqr_batch_4_sve(const float* x, const float* y0, const float* y1, const float* y2, const float* y3, + const size_t d, float& dis0, float& dis1, float& dis2, float& dis3); + +} // namespace faiss +#endif diff --git a/src/simd/hook.cc b/src/simd/hook.cc index a44351577..2b8f9ed56 100644 --- a/src/simd/hook.cc +++ b/src/simd/hook.cc @@ -18,6 +18,10 @@ #include "faiss/FaissHook.h" +#if defined(__ARM_FEATURE_SVE) +#include "distances_sve.h" +#endif + #if defined(__ARM_NEON) #include "distances_neon.h" #endif @@ -137,13 +141,17 @@ enable_patch_for_fp32_bf16() { fvec_L2sqr_batch_4 = fvec_L2sqr_batch_4_ref_bf16_patch; } #endif -#if defined(__ARM_NEON) - fvec_inner_product = fvec_inner_product_neon_bf16_patch; - fvec_L2sqr = fvec_L2sqr_neon_bf16_patch; +#if defined(__aarch64__) - fvec_inner_product_batch_4 = fvec_inner_product_batch_4_neon_bf16_patch; +#if defined(__ARM_NEON) && !defined(__ARM_FEATURE_SVE) + + fvec_L2sqr = fvec_L2sqr_neon_bf16_patch; fvec_L2sqr_batch_4 = fvec_L2sqr_batch_4_neon_bf16_patch; + fvec_inner_product = fvec_inner_product_neon_bf16_patch; + fvec_inner_product_batch_4 = fvec_inner_product_batch_4_neon_bf16_patch; + +#endif #endif } @@ -319,12 +327,42 @@ fvec_hook(std::string& simd_type) { } #endif -#if defined(__ARM_NEON) +#if defined(__aarch64__) + +#if defined(__ARM_FEATURE_SVE) + // ToDo: Enable remaining functions on SVE + + fvec_L2sqr = fvec_L2sqr_sve; + fvec_L1 = fvec_L1_sve; + fvec_Linf = fvec_Linf_sve; + fvec_norm_L2sqr = fvec_norm_L2sqr_sve; + fvec_madd = fvec_madd_sve; + fvec_madd_and_argmin = fvec_madd_and_argmin_sve; + + fvec_inner_product = fvec_inner_product_neon; + fvec_L2sqr_ny = fvec_L2sqr_ny_neon; + fvec_inner_products_ny = fvec_inner_products_ny_neon; + + ivec_inner_product = ivec_inner_product_neon; + ivec_L2sqr = ivec_L2sqr_neon; + + fp16_vec_inner_product = fp16_vec_inner_product_neon; + fp16_vec_L2sqr = fp16_vec_L2sqr_neon; + fp16_vec_norm_L2sqr = fp16_vec_norm_L2sqr_neon; + + bf16_vec_inner_product = bf16_vec_inner_product_neon; + bf16_vec_L2sqr = bf16_vec_L2sqr_neon; + bf16_vec_norm_L2sqr = bf16_vec_norm_L2sqr_neon; + fvec_L2sqr_batch_4 = fvec_L2sqr_batch_4_sve; + simd_type = "SVE"; + support_pq_fast_scan = true; + +#elif defined(__ARM_NEON) + // NEON functions fvec_inner_product = fvec_inner_product_neon; fvec_L2sqr = fvec_L2sqr_neon; fvec_L1 = fvec_L1_neon; fvec_Linf = fvec_Linf_neon; - fvec_norm_L2sqr = fvec_norm_L2sqr_neon; fvec_L2sqr_ny = fvec_L2sqr_ny_neon; fvec_inner_products_ny = fvec_inner_products_ny_neon; @@ -355,6 +393,8 @@ fvec_hook(std::string& simd_type) { #endif +#endif + // ToDo MG: include VSX intrinsics via distances_vsx once _ref tests succeed #if defined(__powerpc64__) fvec_inner_product = fvec_inner_product_ppc; diff --git a/tests/ut/test_knowhere_init.cc b/tests/ut/test_knowhere_init.cc index 0c40a2151..f31f05f07 100644 --- a/tests/ut/test_knowhere_init.cc +++ b/tests/ut/test_knowhere_init.cc @@ -58,7 +58,7 @@ TEST_CASE("Knowhere global config", "[init]") { } TEST_CASE("Knowhere SIMD config", "[simd]") { - std::vector v = {"AVX512", "AVX2", "SSE4_2", "GENERIC", "NEON"}; + std::vector v = {"AVX512", "AVX2", "SSE4_2", "GENERIC", "NEON", "SVE"}; std::unordered_set s(v.begin(), v.end()); auto res = knowhere::KnowhereConfig::SetSimdType(knowhere::KnowhereConfig::SimdType::AVX512);