在 Android 上编译 NEON 代码时出错

Question

这里是简单的二值化函数

void binarize(void *output, const void *input, int begin, int end, uint8_t threshold) {
#ifdef __ARM_NEON__
    uint8x16_t thresholdVector = vdupq_n_u8(threshold);
    uint8x16_t highValueVector = vdupq_n_u8(255);
    uint8x16_t* __restrict inputVector = (uint8x16_t*)input;
    uint8x16_t* __restrict outputVector = (uint8x16_t*)output;
    for ( ; begin < end; begin += 16, ++inputVector, ++outputVector) {
        *outputVector = (*inputVector > thresholdVector) & highValueVector;
    }
#endif
}

它在 iOS 上运行良好。但是，当我为 Android 编译它时，它给了我一个错误：

错误：'uint8x16_t {aka __vector(16) 类型的无效操作数 __builtin_neon_uqi}' 和 'uint8x16_t {aka __vector(16) __builtin_neon_uqi}' 到二进制 'operator>'

我在 Android.mk 中使用这个标志来启用 NEON：

ifeq ($(TARGET_ARCH_ABI),armeabi-v7a)
      LOCAL_ARM_NEON := true
endif

Answer 1

不同之处在于不同的编译器。对于 iOS，您使用 Clang 进行编译，但对于 Android，您使用 GCC 构建代码（除非您覆盖默认值）。

GCC 对向量类型更加愚蠢，不能将它们与 > 或 & 等 C/C++ 运算符一起使用。所以你有两个基本的选择：

1. 尝试使用来自最新 Android NDK r8c 的 Clang 进行编译

   为此，请将NDK_TOOLCHAIN_VERSION=clang3.1 发送到您的Application.mk。

2. 使用vld1q_u8 用于加载，vst1q_u8 用于存储，vcgtq_u8 用于operator > 和vandq_u8 用于operator &，显式重写您的代码