爲什麼編譯器沒有定義__ARM_FEATURE_CRC32？

Question

我一直在研究這個問題一段時間了，我希望有人能指出我的錯誤。我想我無法再通過樹木看到森林了。

我有一個用於測試的LeMaker HiKey開發板。它AArch64，所以其具有NEON和其他CPU的功能，如AES，SHA和CRC32：

$ cat /proc/cpuinfo 
Processor : AArch64 Processor rev 3 (aarch64) 
... 
Features : fp asimd evtstrm aes pmull sha1 sha2 crc32 
... 

當我嘗試編譯的程序：

$ cat test.cxx 
#if (defined(__ARM_NEON__) || defined(__ARM_NEON)) 
# define NEON_INTRINSICS_AVAILABLE 1 
#else 
# define NEON_INTRINSICS_AVAILABLE 0 
#endif 

#if BOOL_NEON_INTRINSICS_AVAILABLE 
# include <arm_neon.h> 
# if defined(__ARM_FEATURE_CRC32) || (__ARM_ACLE >= 200) 
# include <arm_acle.h> 
# endif 
#endif 

#include <stdint.h> 

int main(int argc, char* argv[]) 
{ 
    uint32_t crc = 0; 

    crc = __crc32b(crc, (uint8_t)0); 
    return 0 
} 

這將導致以下：

$ g++ test.cxx -o test.exe 
test.cxx: In function ‘int main(int, char**)’: 
test.cxx:20:33: error: ‘__crc32b’ was not declared in this scope 
    crc = __crc32b(crc, (uint8_t)0); 
           ^
test.cxx:22:1: error: expected ‘;’ before ‘}’ token 
} 
^ 

$ clang++ test.cxx -o test.exe 
test.cxx:20:9: error: use of undeclared identifier '__crc32b' 
    crc = __crc32b(crc, (uint8_t)0); 
     ^
test.cxx:21:11: error: expected ';' after return statement 
    return 0 
     ^
      ; 
2 errors generated. 

文件系統的的grep揭示arm_acle.h實際上頭：

$ grep -IR '__crc32' /usr/lib 
/usr/lib/gcc/.../include/arm_acle.h:__crc32b (uint32_t __a, uint8_t __b) 
... 

並根據ARM® C Language Extensions，第9.7節CRC32本質，當定義__ARM_FEATURE_CRC32時，假設缺失的符號存在。檢查arm_acle.h證實了它。

爲了完整起見，我試着用-march=native編譯，但編譯器拒絕了它。

爲什麼__ARM_FEATURE_CRC32未被編譯器定義？

我能做些什麼來讓程序編譯時使用板上的本地特性？

---

$ gcc --version 
gcc (Debian/Linaro 4.9.2-10) 4.9.2 
Copyright (C) 2014 Free Software Foundation, Inc. 
This is free software; see the source for copying conditions. There is NO 
warranty; not even for MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. 

$ clang --version 
Debian clang version 3.5.0-10 (tags/RELEASE_350/final) (based on LLVM 3.5.0) 
Target: aarch64-unknown-linux-gnu 
Thread model: posix 

---

$ g++ -dM -E - </dev/null | egrep -i '(arm|neon|acle)' 
#define __ARM_NEON 1 

$ clang++ -dM -E - </dev/null | egrep -i '(arm|neon|acle)' 
#define __ARM_64BIT_STATE 1 
#define __ARM_ACLE 200 
#define __ARM_ALIGN_MAX_STACK_PWR 4 
#define __ARM_ARCH 8 
#define __ARM_ARCH_ISA_A64 1 
#define __ARM_ARCH_PROFILE 'A' 
#define __ARM_FEATURE_CLZ 1 
#define __ARM_FEATURE_DIV 1 
#define __ARM_FEATURE_FMA 1 
#define __ARM_FEATURE_UNALIGNED 1 
#define __ARM_FP 0xe 
#define __ARM_FP16_FORMAT_IEEE 1 
#define __ARM_FP_FENV_ROUNDING 1 
#define __ARM_NEON 1 
#define __ARM_NEON_FP 0xe 
#define __ARM_PCS_AAPCS64 1 
#define __ARM_SIZEOF_MINIMAL_ENUM 4 
#define __ARM_SIZEOF_WCHAR_T 4 

Answer 1

至於爲什麼這個功能默認不啓用;這是您的編譯器所針對的基準ABI中不存在的可選功能，即編譯器生成的二進制文件預計能夠在缺乏CRC功能的設備上運行。

至少對於GCC，您可以啓用此功能與-march修改crc，像這樣：

$ gcc -dM -E - -march=armv8-a+crc < /dev/null | egrep -i '(arm|neon|acle|crc)' 
#define __ARM_FEATURE_CRC32 1 
#define __ARM_NEON 1 

關於如何設置多個文檔見https://gcc.gnu.org/onlinedocs/gcc-6.1.0/gcc/AArch64-Options.html（或舊版本的GCC在同一頁） 。

我想人們可以預期-march=native也這樣做，但是目前這個選項似乎只能用於x86架構。