ARM 內建函式

Microsoft C++ 編譯程式 （MSVC） 可在 ARM 架構上使用下列內部函數。 如需 ARM 的詳細資訊，請參閱 ARM 開發人員文件網站的架構和軟體開發工具章節。

氖

ARM 的 NEON 向量指令集延伸模組提供與 x86 和 x64 架構處理器通用之 MMX 和 SSE 向量指令集中的單一指令多重數據 （SIMD） 功能。

支援 NEON 內建函式，並提供於標頭檔 arm_neon.h 中。 NEON 內部函數的 MSVC 支援類似於 ARM 編譯程式，如 ARM Infocenter 網站上的 ARM 編譯程式工具鏈附錄 G 中所述。

MSVC 與 ARM 編譯程式之間的主要差異在於 MSVC 會新增 _ex 和 vstX 向量載入的vldX變體，並儲存指示。 _ex 變異採取額外的參數，以指定指標引數的對齊，除此之外，與非 _ex 對應項目均相同。

ARM 特定的內部函數清單

[返回頂端]

記憶體屏障限制

內部函 __dmb 式（數據記憶體屏障）、 __dsb （資料同步屏障）和 __isb （指令同步處理屏障）會使用下列預先定義的值來指定共用網域的記憶體屏障限制，以及受作業影響的存取類型。

對於 __isb 內建函式，目前唯一有效的限制是 _ARM_BARRIER_SY。架構保留其他所有值。

__iso_volatile_load/存放內部函數

這些內部函數會明確執行不受編譯程式優化影響的載入和存放區。

__int16 __iso_volatile_load16(const volatile __int16 * Location);
__int32 __iso_volatile_load32(const volatile __int32 * Location);
__int64 __iso_volatile_load64(const volatile __int64 * Location);
__int8 __iso_volatile_load8(const volatile __int8 * Location);

void __iso_volatile_store16(volatile __int16 * Location, __int16 Value);
void __iso_volatile_store32(volatile __int32 * Location, __int32 Value);
void __iso_volatile_store64(volatile __int64 * Location, __int64 Value);
void __iso_volatile_store8(volatile __int8 * Location, __int8 Value);

參數

地點
要讀取或寫入的記憶體位置的位址。

ReplTest1
要寫入指定記憶體位置的值（僅儲存內部函數）。

傳回值（僅載入內部函數）

Location 所指定之記憶體位置的值。

備註

您可以使用 __iso_volatile_load8/16/32/64 和 __iso_volatile_store8/16/32/64 內建來明確執行不受編譯程式優化影響的記憶體存取。 編譯程式無法移除、合成或變更這些作業的相對順序，但不會產生隱含的硬體記憶體屏障。 因此，硬體可能仍然重新排列跨多個執行緒中可觀察到的記憶體存取。 更精確地說，這些內部函數相當於在 /volatile：iso 下編譯的下列表達式。

int a = __iso_volatile_load32(p);    // equivalent to: int a = *(const volatile __int32*)p;
__iso_volatile_store32(p, a);        // equivalent to: *(volatile __int32*)p = a;

請注意，內建函式採取暫時性 (volatile) 指標以容納暫時性變數。 不過，不需要或建議使用揮發性指標作為自變數。 如果使用一般、非揮發性型別，這些作業的語意就完全相同。

如需 /volatile：iso 命令行自變數的詳細資訊，請參閱 /volatile （volatile 關鍵詞解譯） 。

_MoveFromCoprocessor，_MoveFromCoprocessor2

這些內建函式會使用副處理器資料傳輸指令，從 ARM 副處理器讀取資料。

int _MoveFromCoprocessor(
      unsigned int coproc,
      unsigned int opcode1,
      unsigned int crn,
      unsigned int crm,
      unsigned int opcode2
);

int _MoveFromCoprocessor2(
      unsigned int coproc,
      unsigned int opcode1,
      unsigned int crn,
      unsigned int crm,
      unsigned int opcode2
);

參數

coproc
副處理器數目，範圍在 0 到 15 之間。

opcode1
範圍 0 到 7 的副處理器專用作業碼

crn
副處理器暫存器編號，範圍介於 0 到 15，指定第一個指令的運算元。

crm
副處理器暫存器數目 (範圍在 0 到 15 之間)，用以指定其他來源或目的地運算元。

opcode2
範圍 0 到 7 的其他副處理器專用作業碼。

傳回值

從副處理器讀取的值。

備註

內建所有五個參數的值必須是編譯時期已知的常數表達式。

_MoveFromCoprocessor 使用 MRC 指令；_MoveFromCoprocessor2 使用 MRC2。 對應到位元欄位的參數，這些參數會直接編碼到指令文字中。 參數的解譯會因副處理器而異。 如需詳細資訊，請參閱該副處理器的手冊。

_MoveFromCoprocessor64

使用副處理器資料傳輸指令，讀取 ARM 副處理器的資料。

unsigned __int64 _MoveFromCoprocessor64(
      unsigned int coproc,
      unsigned int opcode1,
      unsigned int crm,
);

參數

coproc
副處理器數目，範圍在 0 到 15 之間。

opcode1
範圍 0 到 15 的副處理器專用作業碼。

crm
副處理器暫存器數目 (範圍在 0 到 15 之間)，用以指定其他來源或目的地運算元。

傳回值

從副處理器讀取的值。

備註

內建這三個參數的值必須是編譯時期已知的常數表達式。

_MoveFromCoprocessor64 使用 MRRC 指令。 對應到位元欄位的參數，這些參數會直接編碼到指令文字中。 參數的解譯會因副處理器而異。 如需詳細資訊，請參閱該副處理器的手冊。

_MoveToCoprocessor，_MoveToCoprocessor2

這些內建函式會使用副處理器資料傳輸指令，將資料寫入 ARM 副處理器。

void _MoveToCoprocessor(
      unsigned int value,
      unsigned int coproc,
      unsigned int opcode1,
      unsigned int crn,
      unsigned int crm,
      unsigned int opcode2
);

void _MoveToCoprocessor2(
      unsigned int value,
      unsigned int coproc,
      unsigned int opcode1,
      unsigned int crn,
      unsigned int crm,
      unsigned int opcode2
);

參數

value
要寫入副處理器的值。

coproc
副處理器數目，範圍在 0 到 15 之間。

opcode1
範圍 0 到 7 的副處理器專用 opcode。

crn
副處理器暫存器編號，範圍介於 0 到 15，指定第一個指令的運算元。

crm
副處理器暫存器數目 (範圍在 0 到 15 之間)，用以指定其他來源或目的地運算元。

opcode2
範圍 0 到 7 的其他副處理器專用作業碼。

傳回值

無。

備註

內部函數的coproc、 opcode1、 、 crncrm和 opcode2 參數的值必須是編譯時期已知的常數表示式。

_MoveToCoprocessor 使用 MCR 指令；_MoveToCoprocessor2 使用 MCR2。 對應到位元欄位的參數，這些參數會直接編碼到指令文字中。 參數的解譯會因副處理器而異。 如需詳細資訊，請參閱該副處理器的手冊。

_MoveToCoprocessor64

這些內建函式會使用副處理器資料傳輸指令，將資料寫入 ARM 副處理器。

void _MoveFromCoprocessor64(
      unsigned __int64 value,
      unsigned int coproc,
      unsigned int opcode1,
      unsigned int crm,
);

參數

coproc
副處理器數目，範圍在 0 到 15 之間。

opcode1
範圍 0 到 15 的副處理器專用作業碼。

crm
副處理器暫存器數目 (範圍在 0 到 15 之間)，用以指定其他來源或目的地運算元。

傳回值

無。

備註

內部函數的 coproc、 opcode1和 crm 參數的值必須是編譯時期已知的常數表示式。

_MoveFromCoprocessor64 使用 MCRR 指令。 對應到位元欄位的參數，這些參數會直接編碼到指令文字中。 參數的解譯會因副處理器而異。 如需詳細資訊，請參閱該副處理器的手冊。

其他架構內部函數的ARM支援

下表列出 ARM 平台支援的其他架構的內建函式。 其中註明了內建函式的行為在 ARM 上與在其他硬體架構上有哪些不同的其他詳細資料。

[返回頂端]

內建聯結

連鎖內建函式是一組內建函式，用來執行不可部分完成的讀取-修改-寫入作業。 其中有部分通用於所有平台。 它們會分別列在這裡，因為有大量的它們，但由於其定義大多是多餘的，所以一般情況下更容易思考它們。 它們的名稱可以用來得出確切的行為。

下表摘要說明非位元測試連鎖內建函式的 ARM 的支援。 在表中的每個儲存格對應的名稱，是將列的最左邊儲存格的作業名稱，和欄的最上方儲存格的類型名稱，附加至 _Interlocked 所衍生的名稱。 例如，數據列和數據行交集 Xor 處的 8 單元格會對應至 _InterlockedXor8 且完全支援。 大部分受支援的函式會提供這些選擇性的字尾：_acq、_rel 和 _nf。 _acq 字尾表示「取得」語意，_rel 字尾表示「釋放」語意。 _nf或 「無柵欄」後綴對 ARM 而言是唯一的，下一節會討論。

金鑰：

• 完整：支援純文字、 _acq、、 _rel 和 _nf 表單。

• Partial：支援純文本、 _acq和 _nf 窗體。

• 無：不支援

_nf （沒有柵欄） 後綴

_nf或「無柵欄」後綴表示作業不會作為任何種類的記憶體屏障，與其他三種形式（純文本、_acq和_rel）相反，它們的行為都是某種障礙。 表單的 _nf 其中一個可能用法是維護由多個線程同時更新的統計數據計數器，但是其值不會在執行多個線程時使用。

內建聯結的清單

[返回頂端]

_interlockedbittest內部函數

所有平臺通用的一般聯結位測試內部函數。 ARM 會新增 _acq、 _rel和 _nf 變體，其只會修改作業的屏障語意，如本文稍早_nf（無柵欄）後綴所述。

[返回頂端]

另請參閱

編譯器內建函式
ARM64 內部函數
ARM 組合語言程式參考
C++ 語言參考