ARM 內建

發行項
06/10/2015

Visual C++ 編譯器讓 ARM 架構上可使用下列內建函式。如需有關 ARM 的詳細資訊，請參閱 ARM 資訊中心網站的 ARM 架構參考手冊和 ARM 組譯工具指南。

NEON

ARM NEON 向量指令集擴充功能，提供類似通用於 x86 和 x64 架構處理器的 MMX 和 SSE 向量指令集中的單一指令多重資料 (SIMD) 功能。

支援 NEON 內建函式，並提供於標頭檔 arm_neon.h 中。 NEON 內建函式的 Visual C++ 編譯器支援類似 ARM 編譯器，而其已記錄在ARM 資訊中心網站上＜附錄 G＞的 ARM 編譯器工具鏈版本 4.1 編譯器參考。

Visual C++ 編譯器及 ARM 編譯器的主要差異在於，Visual C++ 編譯器加入了 vldX 和 vstX 向量載入和儲存指令的 _ex 變異。 _ex 變異採取額外的參數，以指定指標引數的對齊，除此之外，與非 _ex 對應項目均相同。

ARM 專屬內建函式清單

函式名稱	指令	函式原型
_arm_smlal	SMLAL	__int64 _arm_smlal(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_umlal	UMLAL	unsigned __int64 _arm_umlal(unsigned __int64 _RdHiLo, unsigned int _Rn, unsigned int _Rm)
_arm_clz	CLZ	unsigned int _arm_clz(unsigned int _Rm)
_arm_qadd	QADD	int _arm_qadd(int _Rm, int _Rn)
_arm_qdadd	QDADD	int _arm_qdadd(int _Rm, int _Rn)
_arm_qdsub	QDSUB	int _arm_qdsub(int _Rm, int _Rn)
_arm_qsub	QSUB	int _arm_qsub(int _Rm, int _Rn)
_arm_smlabb	SMLABB	int _arm_smlabb(int _Rn, int _Rm, int _Ra)
_arm_smlabt	SMLABT	int _arm_smlabt(int _Rn, int _Rm, int _Ra)
_arm_smlatb	SMLATB	int _arm_smlatb(int _Rn, int _Rm, int _Ra)
_arm_smlatt	SMLATT	int _arm_smlatt(int _Rn, int _Rm, int _Ra)
_arm_smlalbb	SMLALBB	__int64 _arm_smlalbb(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_smlalbt	SMLALBT	__int64 _arm_smlalbt(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_smlaltb	SMLALTB	__int64 _arm_smlaltb(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_smlaltt	SMLALTT	__int64 _arm_smlaltt(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_smlawb	SMLAWB	int _arm_smlawb(int _Rn, int _Rm, int _Ra)
_arm_smlawt	SMLAWT	int _arm_smlawt(int _Rn, int _Rm, int _Ra)
_arm_smulbb	SMULBB	int _arm_smulbb(int _Rn, int _Rm)
_arm_smulbt	SMULBT	int _arm_smulbt(int _Rn, int _Rm)
_arm_smultb	SMULTB	int _arm_smultb(int _Rn, int _Rm)
_arm_smultt	SMULTT	int _arm_smultt(int _Rn, int _Rm)
_arm_smulwb	SMULWB	int _arm_smulwb(int _Rn, int _Rm)
_arm_smulwt	SMULWT	int _arm_smulwt(int _Rn, int _Rm)
_arm_sadd16	SADD16	int _arm_sadd16(int _Rn, int _Rm)
_arm_sadd8	SADD8	int _arm_sadd8(int _Rn, int _Rm)
_arm_sasx	SASX	int _arm_sasx(int _Rn, int _Rm)
_arm_ssax	SSAX	int _arm_ssax(int _Rn, int _Rm)
_arm_ssub16	SSUB16	int _arm_ssub16(int _Rn, int _Rm)
_arm_ssub8	SSUB8	int _arm_ssub8(int _Rn, int _Rm)
_arm_shadd16	SHADD16	int _arm_shadd16(int _Rn, int _Rm)
_arm_shadd8	SHADD8	int _arm_shadd8(int _Rn, int _Rm)
_arm_shasx	SHASX	int _arm_shasx(int _Rn, int _Rm)
_arm_shsax	SHSAX	int _arm_shsax(int _Rn, int _Rm)
_arm_shsub16	SHSUB16	int _arm_shsub16(int _Rn, int _Rm)
_arm_shsub8	SHSUB8	int _arm_shsub8(int _Rn, int _Rm)
_arm_qadd16	QADD16	int _arm_qadd16(int _Rn, int _Rm)
_arm_qadd8	QADD8	int _arm_qadd8(int _Rn, int _Rm)
_arm_qasx	QASX	int _arm_qasx(int _Rn, int _Rm)
_arm_qsax	QSAX	int _arm_qsax(int _Rn, int _Rm)
_arm_qsub16	QSUB16	int _arm_qsub16(int _Rn, int _Rm)
_arm_qsub8	QSUB8	int _arm_qsub8(int _Rn, int _Rm)
_arm_uadd16	UADD16	unsigned int _arm_uadd16(unsigned int _Rn, unsigned int _Rm)
_arm_uadd8	UADD8	unsigned int _arm_uadd8(unsigned int _Rn, unsigned int _Rm)
_arm_uasx	UASX	unsigned int _arm_uasx(unsigned int _Rn, unsigned int _Rm)
_arm_usax	USAX	unsigned int _arm_usax(unsigned int _Rn, unsigned int _Rm)
_arm_usub16	USUB16	unsigned int _arm_usub16(unsigned int _Rn, unsigned int _Rm)
_arm_usub8	USUB8	unsigned int _arm_usub8(unsigned int _Rn, unsigned int _Rm)
_arm_uhadd16	UHADD16	unsigned int _arm_uhadd16(unsigned int _Rn, unsigned int _Rm)
_arm_uhadd8	UHADD8	unsigned int _arm_uhadd8(unsigned int _Rn, unsigned int _Rm)
_arm_uhasx	UHASX	unsigned int _arm_uhasx(unsigned int _Rn, unsigned int _Rm)
_arm_uhsax	UHSAX	unsigned int _arm_uhsax(unsigned int _Rn, unsigned int _Rm)
_arm_uhsub16	UHSUB16	unsigned int _arm_uhsub16(unsigned int _Rn, unsigned int _Rm)
_arm_uhsub8	UHSUB8	unsigned int _arm_uhsub8(unsigned int _Rn, unsigned int _Rm)
_arm_uqadd16	UQADD16	unsigned int _arm_uqadd16(unsigned int _Rn, unsigned int _Rm)
_arm_uqadd8	UQADD8	unsigned int _arm_uqadd8(unsigned int _Rn, unsigned int _Rm)
_arm_uqasx	UQASX	unsigned int _arm_uqasx(unsigned int _Rn, unsigned int _Rm)
_arm_uqsax	UQSAX	unsigned int _arm_uqsax(unsigned int _Rn, unsigned int _Rm)
_arm_uqsub16	UQSUB16	unsigned int _arm_uqsub16(unsigned int _Rn, unsigned int _Rm)
_arm_uqsub8	UQSUB8	unsigned int _arm_uqsub8(unsigned int _Rn, unsigned int _Rm)
_arm_sxtab	SXTAB	int _arm_sxtab(int _Rn, int _Rm, unsigned int _Rotation)
_arm_sxtab16	SXTAB16	int _arm_sxtab16(int _Rn, int _Rm, unsigned int _Rotation)
_arm_sxtah	SXTAH	int _arm_sxtah(int _Rn, int _Rm, unsigned int _Rotation)
_arm_uxtab	UXTAB	unsigned int _arm_uxtab(unsigned int _Rn, unsigned int _Rm, unsigned int _Rotation)
_arm_uxtab16	UXTAB16	unsigned int _arm_uxta16b(unsigned int _Rn, unsigned int _Rm, unsigned int _Rotation)
_arm_uxtah	UXTAH	unsigned int _arm_uxtah(unsigned int _Rn, unsigned int _Rm, unsigned int _Rotation)
_arm_sxtb	SXTB	int _arm_sxtb(int _Rn, unsigned int _Rotation)
_arm_sxtb16	SXTB16	int _arm_sxtb16(int _Rn, unsigned int _Rotation)
_arm_sxth	SXTH	int _arm_sxth(int _Rn, unsigned int _Rotation)
_arm_uxtb	UXTB	unsigned int _arm_uxtb(unsigned int _Rn, unsigned int _Rotation)
_arm_uxtb16	UXTB16	unsigned int _arm_uxtb16(unsigned int _Rn, unsigned int _Rotation)
_arm_uxth	UXTH	unsigned int _arm_uxth(unsigned int _Rn, unsigned int _Rotation)
_arm_pkhbt	PKHBT	int _arm_pkhbt(int _Rn, int _Rm, unsigned int _Lsl_imm)
_arm_pkhtb	PKHTB	int _arm_pkhtb(int _Rn, int _Rm, unsigned int _Asr_imm)
_arm_usad8	USAD8	unsigned int _arm_usad8(unsigned int _Rn, unsigned int _Rm)
_arm_usada8	USADA8	unsigned int _arm_usada8(unsigned int _Rn, unsigned int _Rm, unsigned int _Ra)
_arm_ssat	SSAT	int _arm_ssat(unsigned int _Sat_imm, _int _Rn, _ARMINTR_SHIFT_T _Shift_type, unsigned int _Shift_imm)
_arm_usat	USAT	int _arm_usat(unsigned int _Sat_imm, _int _Rn, _ARMINTR_SHIFT_T _Shift_type, unsigned int _Shift_imm)
_arm_ssat16	SSAT16	int _arm_ssat16(unsigned int _Sat_imm, _int _Rn)
_arm_usat16	USAT16	int _arm_usat16(unsigned int _Sat_imm, _int _Rn)
_arm_rev	REV	unsigned int _arm_rev(unsigned int _Rm)
_arm_rev16	REV16	unsigned int _arm_rev16(unsigned int _Rm)
_arm_revsh	REVSH	unsigned int _arm_revsh(unsigned int _Rm)
_arm_smlad	SMLAD	int _arm_smlad(int _Rn, int _Rm, int _Ra)
_arm_smladx	SMLADX	int _arm_smladx(int _Rn, int _Rm, int _Ra)
_arm_smlsd	SMLSD	int _arm_smlsd(int _Rn, int _Rm, int _Ra)
_arm_smlsdx	SMLSDX	int _arm_smlsdx(int _Rn, int _Rm, int _Ra)
_arm_smmla	SMMLA	int _arm_smmla(int _Rn, int _Rm, int _Ra)
_arm_smmlar	SMMLAR	int _arm_smmlar(int _Rn, int _Rm, int _Ra)
_arm_smmls	SMMLS	int _arm_smmls(int _Rn, int _Rm, int _Ra)
_arm_smmlsr	SMMLSR	int _arm_smmlsr(int _Rn, int _Rm, int _Ra)
_arm_smmul	SMMUL	int _arm_smmul(int _Rn, int _Rm)
_arm_smmulr	SMMULR	int _arm_smmulr(int _Rn, int _Rm)
_arm_smlald	SMLALD	__int64 _arm_smlald(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_smlaldx	SMLALDX	__int64 _arm_smlaldx(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_smlsld	SMLSLD	__int64 _arm_smlsld(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_smlsldx	SMLSLDX	__int64 _arm_smlsldx(__int64 _RdHiLo, int _Rn, int _Rm)
_arm_smuad	SMUAD	int _arm_smuad(int _Rn, int _Rm)
_arm_smuadx	SMUADX	int _arm_muadxs(int _Rn, int _Rm)
_arm_smusd	SMUSD	int _arm_smusd(int _Rn, int _Rm)
_arm_smusdx	SMUSDX	int _arm_smusdx(int _Rn, int _Rm)
_arm_smull	SMULL	__int64 _arm_smull(int _Rn, int _Rm)
_arm_umull	UMULL	unsigned __int64 _arm_umull(unsigned int _Rn, unsigned int _Rm)
_arm_umaal	UMAAL	unsigned __int64 _arm_umaal(unsigned int _RdLo, unsigned int _RdHi, unsigned int _Rn, unsigned int _Rm)
_arm_bfc	BFC	unsigned int _arm_bfc(unsigned int _Rd, unsigned int _Lsb, unsigned int _Width)
_arm_bfi	BFI	unsigned int _arm_bfi(unsigned int _Rd, unsigned int _Rn, unsigned int _Lsb, unsigned int _Width)
_arm_rbit	RBIT	unsigned int _arm_rbit(unsigned int _Rm)
_arm_sbfx	SBFX	int _arm_sbfx(int _Rn, unsigned int _Lsb, unsigned int _Width)
_arm_ubfx	UBFX	unsigned int _arm_ubfx(unsigned int _Rn, unsigned int _Lsb, unsigned int _Width)
_arm_sdiv	SDIV	int _arm_sdiv(int _Rn, int _Rm)
_arm_udiv	UDIV	unsigned int _arm_udiv(unsigned int _Rn, unsigned int _Rm)
__cps	CPS	void __cps(unsigned int _Ops, unsigned int _Flags, unsigned int _Mode)
__dmb	DMB	void __dmb(unsigned int _Type) 將記憶體屏障作業插入指令資料流中。參數 _Type 會指定屏障強制執行的限制類型。如需可以強制執行的限制類型的詳細資訊，請參閱記憶體屏障限制。
__dsb	DSB	void __dsb(unsigned int _Type) 將記憶體屏障作業插入指令資料流中。參數 _Type 會指定屏障強制執行的限制類型。如需可以強制執行的限制類型的詳細資訊，請參閱記憶體屏障限制。
__isb	ISB	void __isb(unsigned int _Type) 將記憶體屏障作業插入指令資料流中。參數 _Type 會指定屏障強制執行的限制類型。如需可以強制執行的限制類型的詳細資訊，請參閱記憶體屏障限制。
__emit		void __emit(unsigned __int32 opcode) 將指定的指令，插入由編譯器輸出的指令資料流中。 opcode 的值，必須是在編譯時期已知的常數運算式。指令字組的大小是 16 位元，而且最高有效的 16 位元 opcode 會被忽略。編譯器不會嘗試解譯 opcode 的內容，並在執行插入的指令之前，不會保證 CPU 或記憶體狀態。編譯器假設執行插入指令之後，CPU 和記憶體的狀態為不變。因此，會變更狀態的指令，可能會對由編譯器所產生的一般程式碼，造成不利的影響。基於這個理由，只使用 emit 將會影響編譯器通常不處理的 CPU 狀態 (例如，副處理器狀態) 的指令插入，或用於實作以 declspec(naked) 宣告的函式。
__hvc	HVC	unsigned int __hvc(unsigned int, ...)
__iso_volatile_load16		__int16 __iso_volatile_load16(const volatile __int16 *) 如需詳細資訊，請參閱 __iso_volatile_load/store 內建函式。
__iso_volatile_load32		__int32 __iso_volatile_load32(const volatile __int32 *) 如需詳細資訊，請參閱 __iso_volatile_load/store 內建函式。
__iso_volatile_load64		__int64 __iso_volatile_load64(const volatile __int64 *) 如需詳細資訊，請參閱 __iso_volatile_load/store 內建函式。
__iso_volatile_load8		__int8 __iso_volatile_load8(const volatile __int8 *) 如需詳細資訊，請參閱 __iso_volatile_load/store 內建函式。
__iso_volatile_store16		void __iso_volatile_store16(volatile __int16 *, __int16) 如需詳細資訊，請參閱 __iso_volatile_load/store 內建函式。
__iso_volatile_store32		void __iso_volatile_store32(volatile __int32 *, __int32) 如需詳細資訊，請參閱 __iso_volatile_load/store 內建函式。
__iso_volatile_store64		void __iso_volatile_store64(volatile __int64 *, __int64) 如需詳細資訊，請參閱 __iso_volatile_load/store 內建函式。
__iso_volatile_store8		void __iso_volatile_store8(volatile __int8 *, __int8) 如需詳細資訊，請參閱 __iso_volatile_load/store 內建函式。
__ldrexd	LDREXD	__int64 __ldrexd(const volatile __int64 *)
__prefetch	PLD	void __cdecl __prefetch(const void *) 提供 PLD 記憶體提示給系統，通知可能很快就存取位於或接近指定位址的記憶體。有些系統可能會選擇最佳化此記憶體存取模式，來增加執行階段效能。不過，從 C++ 語言的觀點來看，函式沒有顯著的影響，而且可能根本不執行任何動作。
__rdpmccntr64		unsigned __int64 __rdpmccntr64(void)
__sev	SEV	void __sev(void)
__static_assert		void __static_assert(int, const char *)
__swi	SVC	unsigned int __swi(unsigned int, ...)
__trap	BKPT	int __trap(int, ...)
__wfe	WFE	void __wfe(void)
__wfi	WFI	void __wfi(void)
_AddSatInt	QADD	int _AddSatInt(int, int)
_CopyDoubleFromInt64		double _CopyDoubleFromInt64(__int64)
_CopyFloatFromInt32		float _CopyFloatFromInt32(__int32)
_CopyInt32FromFloat		__int32 _CopyInt32FromFloat(float)
_CopyInt64FromDouble		__int64 _CopyInt64FromDouble(double)
_CountLeadingOnes		unsigned int _CountLeadingOnes(unsigned long)
_CountLeadingOnes64		unsigned int _CountLeadingOnes64(unsigned __int64)
_CountLeadingSigns		unsigned int _CountLeadingSigns(long)
_CountLeadingSigns64		unsigned int _CountLeadingSigns64(__int64)
_CountLeadingZeros		unsigned int _CountLeadingZeros(unsigned long)
_CountLeadingZeros64		unsigned int _CountLeadingZeros64(unsigned __int64)
_CountOneBits		unsigned int _CountOneBits(unsigned long)
_CountOneBits64		unsigned int _CountOneBits64(unsigned __int64)
_DAddSatInt	QDADD	int _DAddSatInt(int, int)
_DSubSatInt	QDSUB	int _DSubSatInt(int, int)
_isunordered		int _isunordered(double, double)
_isunorderedf		int _isunorderedf(float, float)
_MoveFromCoprocessor	MRC	unsigned int _MoveFromCoprocessor(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int) 使用副處理器資料傳輸指令，讀取 ARM 副處理器的資料。如需詳細資訊，請參閱 _MoveFromCoprocessor, _MoveFromCoprocessor2。
_MoveFromCoprocessor2	MRC2	unsigned int _MoveFromCoprocessor2(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int) 使用副處理器資料傳輸指令，讀取 ARM 副處理器的資料。如需詳細資訊，請參閱 _MoveFromCoprocessor, _MoveFromCoprocessor2。
_MoveFromCoprocessor64	MRRC	unsigned __int64 _MoveFromCoprocessor64(unsigned int, unsigned int, unsigned int) 使用副處理器資料傳輸指令，讀取 ARM 副處理器的資料。如需詳細資訊，請參閱 _MoveFromCoprocessor64。
_MoveToCoprocessor	MCR	void _MoveToCoprocessor(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int, unsigned int) 使用副處理器資料傳輸指令，讀取 ARM 副處理器的資料。如需詳細資訊，請參閱 _MoveToCoprocessor, _MoveToCoprocessor2。
_MoveToCoprocessor2	MCR2	void _MoveToCoprocessor2(unsigned int, unsigned int, unsigned int, unsigned int, unsigned int, unsigned int) 使用副處理器資料傳輸指令，讀取 ARM 副處理器的資料。如需詳細資訊，請參閱 _MoveToCoprocessor, _MoveToCoprocessor2。
_MoveToCoprocessor64	MCRR	void _MoveToCoprocessor64(unsigned __int64, unsigned int, unsigned int, unsigned int) 使用副處理器資料傳輸指令，讀取 ARM 副處理器的資料。如需詳細資訊，請參閱 _MoveToCoprocessor64。
_MulHigh		long _MulHigh(long, long)
_MulUnsignedHigh		unsigned long _MulUnsignedHigh(unsigned long, unsigned long)
_ReadBankedReg	MRS	int _ReadBankedReg(int _Reg)
_ReadStatusReg	MRS	int _ReadStatusReg(int)
_SubSatInt	QSUB	int _SubSatInt(int, int)
_WriteBankedReg	MSR	void _WriteBankedReg(int _Value, int _Reg)
_WriteStatusReg	MSR	void _WriteStatusReg(int, int, int)

[回到頁首]

記憶體屏障限制

內建函式 __dmb (資料記憶體屏障) __dsb (資料同步處理屏障) 和 __isb (指令同步處理屏障) 會使用下列預先定義值，指定關於受作業影響之共用網域及存取類型的記憶體屏障限制。

限制值	描述
_ARM_BARRIER_SY	完整系統，讀取和寫入。
_ARM_BARRIER_ST	完整系統，只寫入。
_ARM_BARRIER_ISH	可內部共用，讀取和寫入。
_ARM_BARRIER_ISHST	可內部共用，只寫入。
_ARM_BARRIER_NSH	不可共用，讀取和寫入。
_ARM_BARRIER_NSHST	不可共用，只寫入。
_ARM_BARRIER_OSH	可外部共用，讀取和寫入。
_ARM_BARRIER_OSHST	可外部共用，只寫入。

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

__iso_volatile_load/store 內建函式

這些內建函式會明確地執行不受編譯器最佳化約束的載入和儲存。

__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)

參數

Location
要讀取或寫入的記憶體位置的位址。
Value (僅限儲存內建函式)
要寫入至指定記憶體位置的值。

傳回值 (僅限載入內建函式)

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

備註

您可以使用 __iso_volatile_load8/16/32/64 和 __iso_volatile_store8/16/32/64 內建函式，明確地執行不受編譯器最佳化約束的記憶體存取。編譯器無法移除、合成 (synthetize)，或變更這些作業的相對順序，但不會產生隱含硬體記憶體屏障。因此，硬體可能仍然重新排列跨多個執行緒中可觀察到的記憶體存取。更準確的說，這些內建函式相當於在 /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 的副處理器專用 opcode
crn
副處理器暫存器編號，範圍介於 0 到 15，指定第一個指令的運算元。
crm
副處理器暫存器數目 (範圍在 0 到 15 之間)，用以指定其他來源或目的地運算元。
opcode2
範圍 0 到 7 的其他副處理器專用 opcode。

傳回值

從副處理器讀取的值。

備註

此內建函式的所有五個參數值，必須是在編譯時期已知的常數運算式。

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

_MoveFromCoprocessor64

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

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

參數

coproc
副處理器數目，範圍在 0 到 15 之間。
opcode1
範圍 0 到 15 的副處理器專用 opcode。
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 的其他副處理器專用 opcode。

傳回值

無。

備註

此內建函式的 coproc、opcode1、crn、crm 及 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 的副處理器專用 opcode。
crm
副處理器暫存器數目 (範圍在 0 到 15 之間)，用以指定其他來源或目的地運算元。

傳回值

無。

備註

此內建函式的 coproc、opcode1 及 crm 參數值，必須是在編譯時期已知的常數運算式。

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

來自其他架構之內建函式的 ARM 支援

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

__assume

void __assume(int)

__code_seg

void __code_seg(const char *)

__debugbreak

void __cdecl __debugbreak(void)

__fastfail

__declspec(noreturn) void __fastfail(unsigned int)

__nop

void __nop(void)

ARM 平台上，如果在目標架構實作其中一個函式，這個函式會產生 NOP 指令；否則，會產生不會變更程式或 CPU 狀態的替代指令 — 例如，MOV r8, r8。這在功能上相當於其他硬體架構的內建函式 __nop。

因為最佳化因素，目標架構可能會略過不會影響程式或 CPU 狀態的指令，所以指令不一定會消耗 CPU 週期。因此，請勿使用 __nop 內建函式來管理程式碼順序的執行時間，除非您確定 CPU 會有什麼反應。但您可以使用內建函式 __nop，將下一個指令對齊特定 32 位元的界限位址。

__yield

void __yield(void)

注意事項
在 ARM 平台上，這個函式會產生 YIELD 指令，表示執行緒正在執行的工作可以暫時停止執行 (例如，執行緒同步鎖定)，且不會對程式有不良的影響。這可讓 CPU 在執行週期中執行其他工作，這樣才不會浪費。

_AddressOfReturnAddress

void * _AddressOfReturnAddress(void)

_BitScanForward

unsigned char _BitScanForward(unsigned long * _Index, unsigned long _Mask)

_BitScanReverse

unsigned char _BitScanReverse(unsigned long * _Index, unsigned long _Mask)

_bittest

unsigned char _bittest(long const *, long)

_bittestandcomplement

unsigned char _bittestandcomplement(long *, long)

_bittestandreset

unsigned char _bittestandreset(long *, long)

_bittestandset

unsigned char _bittestandset(long *, long)

_byteswap_uint64

unsigned __int64 __cdecl _byteswap_uint64(unsigned __int64)

_byteswap_ulong

unsigned long __cdecl _byteswap_ulong(unsigned long)

_byteswap_ushort

unsigned short __cdecl _byteswap_ushort(unsigned short)

_disable

void __cdecl _disable(void)

注意事項
ARM 平台上，這個函式會產生 CPSID 指令；其只限於做為內建函式使用。

_enable

void __cdecl _enable(void)

注意事項
ARM 平台上，這個函式會產生 CPSIE 指令；其只限於做為內建函式使用。

_lrotl

unsigned long __cdecl _lrotl(unsigned long, int)

_lrotr

unsigned long __cdecl _lrotr(unsigned long, int)

_ReadBarrier

void _ReadBarrier(void)

_ReadWriteBarrier

void _ReadWriteBarrier(void)

_ReturnAddress

void * _ReturnAddress(void)

_rotl

unsigned int __cdecl _rotl(unsigned int _Value, int _Shift)

_rotl16

unsigned short _rotl16(unsigned short _Value, unsigned char _Shift)

_rotl64

unsigned __int64 __cdecl _rotl64(unsigned __int64 _Value, int _Shift)

_rotl8

unsigned char _rotl8(unsigned char _Value, unsigned char _Shift)

_rotr

unsigned int __cdecl _rotr(unsigned int _Value, int _Shift)

_rotr16

unsigned short _rotr16(unsigned short _Value, unsigned char _Shift)

_rotr64

unsigned __int64 __cdecl _rotr64(unsigned __int64 _Value, int _Shift)

_rotr8

unsigned char _rotr8(unsigned char _Value, unsigned char _Shift)

_setjmpex

int __cdecl _setjmpex(jmp_buf)

_WriteBarrier

void _WriteBarrier(void)

[回到頁首]

連鎖內建函式

連鎖內建函式是一組內建函式，用來執行不可部分完成的讀取-修改-寫入作業。其中有部分通用於所有平台。因為有大量的連鎖內建函式，所以此處分別列出，由於它們的定義通常是重複的，所以很容易引起聯想。它們的名稱可以用來得出確切的行為。

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

	8	16	32	64	P
Add	無	無	全功能	全功能	無
及	全功能	全功能	全功能	全功能	無
CompareExchange	全功能	全功能	全功能	全功能	全功能
遞減	無	全功能	全功能	全功能	無
Exchange	Partial	Partial	Partial	Partial	Partial
ExchangeAdd	全功能	全功能	全功能	全功能	無
遞增	無	全功能	全功能	全功能	無
或	全功能	全功能	全功能	全功能	無
Xor	全功能	全功能	全功能	全功能	無

關鍵字：

完整：支援一般、_acq、_rel 和 _nf 形式。
部分：支援一般、_acq 和 _nf 形式。
無：不支援

_nf (無範圍) 字尾

_nf 或「無範圍」字尾，表示不會以任何記憶體屏障類型進行作業。這是與其他三種形式 (一般、_acq 和 _rel) 的不同之處，其他三種形式都會有屏障類型的行為。有一種 _nf 形式的可能用法，是要維護由多個執行緒同時更新，但多個執行緒正在執行時卻不會使用其值的統計資料計數器。

連鎖內建函式的清單

函式名稱	函式原型
_InterlockedAdd	long _InterlockedAdd(long _volatile *, long)
_InterlockedAdd64	__int64 _InterlockedAdd64(__int64 volatile *, __int64)
_InterlockedAdd64_acq	__int64 _InterlockedAdd64_acq(__int64 volatile *, __int64)
_InterlockedAdd64_nf	__int64 _InterlockedAdd64_nf(__int64 volatile *, __int64)
_InterlockedAdd64_rel	__int64 _InterlockedAdd64_rel(__int64 volatile *, __int64)
_InterlockedAdd_acq	long _InterlockedAdd_acq(long volatile *, long)
_InterlockedAdd_nf	long _InterlockedAdd_nf(long volatile *, long)
_InterlockedAdd_rel	long _InterlockedAdd_rel(long volatile *, long)
_InterlockedAnd	long _InterlockedAnd(long volatile *, long)
_InterlockedAnd16	short _InterlockedAnd16(short volatile *, short)
_InterlockedAnd16_acq	short _InterlockedAnd16_acq(short volatile *, short)
_InterlockedAnd16_nf	short _InterlockedAnd16_nf(short volatile *, short)
_InterlockedAnd16_rel	short _InterlockedAnd16_rel(short volatile *, short)
_InterlockedAnd64	__int64 _InterlockedAnd64(__int64 volatile *, __int64)
_InterlockedAnd64_acq	__int64 _InterlockedAnd64_acq(__int64 volatile *, __int64)
_InterlockedAnd64_nf	__int64 _InterlockedAnd64_nf(__int64 volatile *, __int64)
_InterlockedAnd64_rel	__int64 _InterlockedAnd64_rel(__int64 volatile *, __int64)
_InterlockedAnd8	char _InterlockedAnd8(char volatile *, char)
_InterlockedAnd8_acq	char _InterlockedAnd8_acq(char volatile *, char)
_InterlockedAnd8_nf	char _InterlockedAnd8_nf(char volatile *, char)
_InterlockedAnd8_rel	char _InterlockedAnd8_rel(char volatile *, char)
_InterlockedAnd_acq	long _InterlockedAnd_acq(long volatile *, long)
_InterlockedAnd_nf	long _InterlockedAnd_nf(long volatile *, long)
_InterlockedAnd_rel	long _InterlockedAnd_rel(long volatile *, long)
_InterlockedCompareExchange	long __cdecl _InterlockedCompareExchange(long volatile *, long, long)
_InterlockedCompareExchange16	short _InterlockedCompareExchange16(short volatile *, short, short)
_InterlockedCompareExchange16_acq	short _InterlockedCompareExchange16_acq(short volatile *, short, short)
_InterlockedCompareExchange16_nf	short _InterlockedCompareExchange16_nf(short volatile *, short, short)
_InterlockedCompareExchange16_rel	short _InterlockedCompareExchange16_rel(short volatile *, short, short)
_InterlockedCompareExchange64	__int64 _InterlockedCompareExchange64(__int64 volatile *, __int64, __int64)
_InterlockedCompareExchange64_acq	__int64 _InterlockedCompareExchange64_acq(__int64 volatile *, __int64, __int64)
_InterlockedCompareExchange64_nf	__int64 _InterlockedCompareExchange64_nf(__int64 volatile *, __int64, __int64)
_InterlockedCompareExchange64_rel	__int64 _InterlockedCompareExchange64_rel(__int64 volatile *, __int64, __int64)
_InterlockedCompareExchange8	char _InterlockedCompareExchange8(char volatile *, char, char)
_InterlockedCompareExchange8_acq	char _InterlockedCompareExchange8_acq(char volatile *, char, char)
_InterlockedCompareExchange8_nf	char _InterlockedCompareExchange8_nf(char volatile *, char, char)
_InterlockedCompareExchange8_rel	char _InterlockedCompareExchange8_rel(char volatile *, char, char)
_InterlockedCompareExchangePointer	void * _InterlockedCompareExchangePointer(void * volatile , void , void *)
_InterlockedCompareExchangePointer_acq	void * _InterlockedCompareExchangePointer_acq(void * volatile , void , void *)
_InterlockedCompareExchangePointer_nf	void * _InterlockedCompareExchangePointer_nf(void * volatile , void , void *)
_InterlockedCompareExchangePointer_rel	void * _InterlockedCompareExchangePointer_rel(void * volatile , void , void *)
_InterlockedCompareExchange_acq	long _InterlockedCompareExchange_acq(long volatile *, long, long)
_InterlockedCompareExchange_nf	long _InterlockedCompareExchange_nf(long volatile *, long, long)
_InterlockedCompareExchange_rel	long _InterlockedCompareExchange_rel(long volatile *, long, long)
_InterlockedDecrement	long __cdecl _InterlockedDecrement(long volatile *)
_InterlockedDecrement16	short _InterlockedDecrement16(short volatile *)
_InterlockedDecrement16_acq	short _InterlockedDecrement16_acq(short volatile *)
_InterlockedDecrement16_nf	short _InterlockedDecrement16_nf(short volatile *)
_InterlockedDecrement16_rel	short _InterlockedDecrement16_rel(short volatile *)
_InterlockedDecrement64	__int64 _InterlockedDecrement64(__int64 volatile *)
_InterlockedDecrement64_acq	__int64 _InterlockedDecrement64_acq(__int64 volatile *)
_InterlockedDecrement64_nf	__int64 _InterlockedDecrement64_nf(__int64 volatile *)
_InterlockedDecrement64_rel	__int64 _InterlockedDecrement64_rel(__int64 volatile *)
_InterlockedDecrement_acq	long _InterlockedDecrement_acq(long volatile *)
_InterlockedDecrement_nf	long _InterlockedDecrement_nf(long volatile *)
_InterlockedDecrement_rel	long _InterlockedDecrement_rel(long volatile *)
_InterlockedExchange	long __cdecl _InterlockedExchange(long volatile * _Target, long)
_InterlockedExchange16	short _InterlockedExchange16(short volatile * _Target, short)
_InterlockedExchange16_acq	short _InterlockedExchange16_acq(short volatile * _Target, short)
_InterlockedExchange16_nf	short _InterlockedExchange16_nf(short volatile * _Target, short)
_InterlockedExchange64	__int64 _InterlockedExchange64(__int64 volatile * _Target, __int64)
_InterlockedExchange64_acq	__int64 _InterlockedExchange64_acq(__int64 volatile * _Target, __int64)
_InterlockedExchange64_nf	__int64 _InterlockedExchange64_nf(__int64 volatile * _Target, __int64)
_InterlockedExchange8	char _InterlockedExchange8(char volatile * _Target, char)
_InterlockedExchange8_acq	char _InterlockedExchange8_acq(char volatile * _Target, char)
_InterlockedExchange8_nf	char _InterlockedExchange8_nf(char volatile * _Target, char)
_InterlockedExchangeAdd	long __cdecl _InterlockedExchangeAdd(long volatile *, long)
_InterlockedExchangeAdd16	short _InterlockedExchangeAdd16(short volatile *, short)
_InterlockedExchangeAdd16_acq	short _InterlockedExchangeAdd16_acq(short volatile *, short)
_InterlockedExchangeAdd16_nf	short _InterlockedExchangeAdd16_nf(short volatile *, short)
_InterlockedExchangeAdd16_rel	short _InterlockedExchangeAdd16_rel(short volatile *, short)
_InterlockedExchangeAdd64	__int64 _InterlockedExchangeAdd64(__int64 volatile *, __int64)
_InterlockedExchangeAdd64_acq	__int64 _InterlockedExchangeAdd64_acq(__int64 volatile *, __int64)
_InterlockedExchangeAdd64_nf	__int64 _InterlockedExchangeAdd64_nf(__int64 volatile *, __int64)
_InterlockedExchangeAdd64_rel	__int64 _InterlockedExchangeAdd64_rel(__int64 volatile *, __int64)
_InterlockedExchangeAdd8	char _InterlockedExchangeAdd8(char volatile *, char)
_InterlockedExchangeAdd8_acq	char _InterlockedExchangeAdd8_acq(char volatile *, char)
_InterlockedExchangeAdd8_nf	char _InterlockedExchangeAdd8_nf(char volatile *, char)
_InterlockedExchangeAdd8_rel	char _InterlockedExchangeAdd8_rel(char volatile *, char)
_InterlockedExchangeAdd_acq	long _InterlockedExchangeAdd_acq(long volatile *, long)
_InterlockedExchangeAdd_nf	long _InterlockedExchangeAdd_nf(long volatile *, long)
_InterlockedExchangeAdd_rel	long _InterlockedExchangeAdd_rel(long volatile *, long)
_InterlockedExchangePointer	void * _InterlockedExchangePointer(void * volatile * _Target, void *)
_InterlockedExchangePointer_acq	void * _InterlockedExchangePointer_acq(void * volatile * _Target, void *)
_InterlockedExchangePointer_nf	void * _InterlockedExchangePointer_nf(void * volatile * _Target, void *)
_InterlockedExchange_acq	long _InterlockedExchange_acq(long volatile * _Target, long)
_InterlockedExchange_nf	long _InterlockedExchange_nf(long volatile * _Target, long)
_InterlockedIncrement	long __cdecl _InterlockedIncrement(long volatile *)
_InterlockedIncrement16	short _InterlockedIncrement16(short volatile *)
_InterlockedIncrement16_acq	short _InterlockedIncrement16_acq(short volatile *)
_InterlockedIncrement16_nf	short _InterlockedIncrement16_nf(short volatile *)
_InterlockedIncrement16_rel	short _InterlockedIncrement16_rel(short volatile *)
_InterlockedIncrement64	__int64 _InterlockedIncrement64(__int64 volatile *)
_InterlockedIncrement64_acq	__int64 _InterlockedIncrement64_acq(__int64 volatile *)
_InterlockedIncrement64_nf	__int64 _InterlockedIncrement64_nf(__int64 volatile *)
_InterlockedIncrement64_rel	__int64 _InterlockedIncrement64_rel(__int64 volatile *)
_InterlockedIncrement_acq	long _InterlockedIncrement_acq(long volatile *)
_InterlockedIncrement_nf	long _InterlockedIncrement_nf(long volatile *)
_InterlockedIncrement_rel	long _InterlockedIncrement_rel(long volatile *)
_InterlockedOr	long _InterlockedOr(long volatile *, long)
_InterlockedOr16	short _InterlockedOr16(short volatile *, short)
_InterlockedOr16_acq	short _InterlockedOr16_acq(short volatile *, short)
_InterlockedOr16_nf	short _InterlockedOr16_nf(short volatile *, short)
_InterlockedOr16_rel	short _InterlockedOr16_rel(short volatile *, short)
_InterlockedOr64	__int64 _InterlockedOr64(__int64 volatile *, __int64)
_InterlockedOr64_acq	__int64 _InterlockedOr64_acq(__int64 volatile *, __int64)
_InterlockedOr64_nf	__int64 _InterlockedOr64_nf(__int64 volatile *, __int64)
_InterlockedOr64_rel	__int64 _InterlockedOr64_rel(__int64 volatile *, __int64)
_InterlockedOr8	char _InterlockedOr8(char volatile *, char)
_InterlockedOr8_acq	char _InterlockedOr8_acq(char volatile *, char)
_InterlockedOr8_nf	char _InterlockedOr8_nf(char volatile *, char)
_InterlockedOr8_rel	char _InterlockedOr8_rel(char volatile *, char)
_InterlockedOr_acq	long _InterlockedOr_acq(long volatile *, long)
_InterlockedOr_nf	long _InterlockedOr_nf(long volatile *, long)
_InterlockedOr_rel	long _InterlockedOr_rel(long volatile *, long)
_InterlockedXor	long _InterlockedXor(long volatile *, long)
_InterlockedXor16	short _InterlockedXor16(short volatile *, short)
_InterlockedXor16_acq	short _InterlockedXor16_acq(short volatile *, short)
_InterlockedXor16_nf	short _InterlockedXor16_nf(short volatile *, short)
_InterlockedXor16_rel	short _InterlockedXor16_rel(short volatile *, short)
_InterlockedXor64	__int64 _InterlockedXor64(__int64 volatile *, __int64)
_InterlockedXor64_acq	__int64 _InterlockedXor64_acq(__int64 volatile *, __int64)
_InterlockedXor64_nf	__int64 _InterlockedXor64_nf(__int64 volatile *, __int64)
_InterlockedXor64_rel	__int64 _InterlockedXor64_rel(__int64 volatile *, __int64)
_InterlockedXor8	char _InterlockedXor8(char volatile *, char)
_InterlockedXor8_acq	char _InterlockedXor8_acq(char volatile *, char)
_InterlockedXor8_nf	char _InterlockedXor8_nf(char volatile *, char)
_InterlockedXor8_rel	char _InterlockedXor8_rel(char volatile *, char)
_InterlockedXor_acq	long _InterlockedXor_acq(long volatile *, long)
_InterlockedXor_nf	long _InterlockedXor_nf(long volatile *, long)
_InterlockedXor_rel	long _InterlockedXor_rel(long volatile *, long)

[回到頁首]

_interlockedbittest 內建函式

一般的連鎖位元測試內建函式是通用於所有平台。 ARM 加入了 _acq、_rel 和 _nf 變數，而這只是修改屏障的作業語意，如稍早在本文的 _nf (無範圍) 字尾中所述。

函式名稱	函式原型
_interlockedbittestandreset	unsigned char _interlockedbittestandreset(long volatile *, long)
_interlockedbittestandreset_acq	unsigned char _interlockedbittestandreset_acq(long volatile *, long)
_interlockedbittestandreset_nf	unsigned char _interlockedbittestandreset_nf(long volatile *, long)
_interlockedbittestandreset_rel	unsigned char _interlockedbittestandreset_rel(long volatile *, long)
_interlockedbittestandset	unsigned char _interlockedbittestandset(long volatile *, long)
_interlockedbittestandset_acq	unsigned char _interlockedbittestandset_acq(long volatile *, long)
_interlockedbittestandset_nf	unsigned char _interlockedbittestandset_nf(long volatile *, long)
_interlockedbittestandset_rel	unsigned char _interlockedbittestandset_rel(long volatile *, long)

[回到頁首]

請參閱

參考

編譯器內建

其他資源

ARM 組合程式參考

C++ 語言參考

共用方式為

ARM 內建

NEON

ARM 專屬內建函式清單

記憶體屏障限制

__iso_volatile_load/store 內建函式

_MoveFromCoprocessor, _MoveFromCoprocessor2

_MoveFromCoprocessor64

_MoveToCoprocessor, _MoveToCoprocessor2

_MoveToCoprocessor64

來自其他架構之內建函式的 ARM 支援

連鎖內建函式

_nf (無範圍) 字尾

連鎖內建函式的清單

_interlockedbittest 內建函式

請參閱

參考

其他資源

其他資源