ARM – vnitřní funkce

Kompilátor jazyka Microsoft C++ (MSVC) získejte v architektuře ARM následující vnitřní funkce. Další informace o ARM najdete v částech Nástroje pro architekturu a vývoj softwaru na webu dokumentace pro vývojáře ARM.

NEON

Rozšíření sady vektorových instrukcí NEON pro ARM poskytují funkce Single Instruction Multiple Data (SIMD), které se podobají funkcím v sadách vektorových instrukcí MMX a SSE, které jsou společné pro procesory architektury x86 a x64.

Funkce NEON jsou podporovány, jak je k dispozici v souboru hlaviček arm_neon.h . Podpora MSVC NEON se podobá podpoře kompilátoru ARM, která je zdokumentovaná v Příloze G sady nástrojů kompilátoru ARM, Reference kompilátoru verze 4.1 na webu informačního centra ARM.

Hlavní rozdíl mezi MSVC a kompilátorem ARM spočívá v tom, že MSVC přidává varianty vektorového načtení a uložení instrukcí _exvldX a vstX . Varianty převezměte další parametr, který určuje zarovnání argumentu ukazatele, ale jsou jinak identické s jejich _ex protějšky, které nejsou _ex protějšky.

Výpis vnitřních objektů specifických pro ARM

[Návrat k hornímu]

Omezení bariéry paměti

Vnitřní funkce __dmb (překážka datové paměti), __dsb (bariéra synchronizace dat) a __isb (bariéra synchronizace instrukcí) používají následující předdefinované hodnoty k určení omezení bariéry paměti v souvislosti s doménou sdílení a druhem přístupu, na který je tato operace ovlivněna.

Pro __isb vnitřní je jediné omezení, které je aktuálně platné, _ARM_BARRIER_SY. všechny ostatní hodnoty jsou rezervovány architekturou.

__iso_volatile_load vnitřní objekty/Store

Tyto vnitřní funkce explicitně provádějí zatížení a obchody, které nepodléhají optimalizacím kompilátoru.

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

Parametry

Umístění
Adresa umístění v paměti pro čtení nebo zápis.

Hodnota
Hodnota, která se má zapsat do určeného umístění v paměti (jenom vnitřní objekty úložiště)

Návratová hodnota (jenom vnitřní načtení)

Hodnota umístění v paměti, která je určena parametrem Location .

Poznámky

__iso_volatile_load8/16/32/64Vnitřní objekty a můžete použít __iso_volatile_store8/16/32/64 k explicitnímu provádění přístupů do paměti, které nepodléhají optimalizacím kompilátoru. Kompilátor nemůže odebrat, synthetize ani změnit relativní pořadí těchto operací, ale negeneruje implicitní překážky hardwarové paměti. Proto může hardware stále změnit pořadí pozorovatelných přístupů k paměti ve více vláknech. Přesněji jsou tyto vnitřní prvky rovnocenné následujícím výrazům, jak je zkompilováno v /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;

Všimněte si, že vnitřní objekty využívají nestálé ukazatele, aby vyhovovaly nestálým proměnným. Neexistuje ale žádný požadavek nebo doporučení, aby jako argumenty používaly nestálé ukazatele. Sémantika těchto operací je přesně stejná, pokud je použit běžný, nestálý typ.

Další informace o argumentu příkazového řádku /volatile: ISO najdete v tématu /volatile (nestálá interpretace klíčových slov).

_MoveFromCoprocessor _MoveFromCoprocessor2

Tyto vnitřní funkce čtou data ze spoluprocesorů ARM pomocí instrukcí pro přenos dat koprocesorů.

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

Parametry

koprocedura
Číslo koprocesoru v rozsahu 0 až 15.

opcode1
Operační kód pro procesor specifický pro procesor v rozsahu od 0 do 7

crn
Číslo registru koprocesoru v rozsahu 0 až 15, který určuje první operand instrukce.

crm
Číslo registru koprocesoru v rozsahu 0 až 15, který určuje další zdrojový nebo cílový operand.

opcode2
Další operační kód pro procesor specifický pro procesor v rozsahu od 0 do 7.

Vrácená hodnota

Hodnota, která je čtena ze spoluprocesoru.

Poznámky

Hodnoty všech pěti parametrů vnitřní musí být konstantní výrazy, které jsou známy v době kompilace.

_MoveFromCoprocessor používá instrukci MRC; _MoveFromCoprocessor2 používá MRC2. Parametry odpovídají bitová poleům, které jsou zakódovány přímo v pokynovém slově. Interpretace parametrů je závislá na koprocesoru. Další informace najdete v příručce k příslušnému spoluprocesoru.

_MoveFromCoprocessor64

Čte data ze spoluprocesorů ARM pomocí instrukcí pro přenos dat koprocesorů.

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

Parametry

koprocedura
Číslo koprocesoru v rozsahu 0 až 15.

opcode1
Operační kód pro procesor specifický pro procesor v rozsahu 0 až 15.

crm
Číslo registru koprocesoru v rozsahu 0 až 15, který určuje další zdrojový nebo cílový operand.

Vrácená hodnota

Hodnota, která je čtena ze spoluprocesoru.

Poznámky

Hodnoty všech tří parametrů vnitřní musí být konstantní výrazy, které jsou známy v době kompilace.

_MoveFromCoprocessor64 používá instrukci MRRC. Parametry odpovídají bitová poleům, které jsou zakódovány přímo v pokynovém slově. Interpretace parametrů je závislá na koprocesoru. Další informace najdete v příručce k příslušnému spoluprocesoru.

_MoveToCoprocessor _MoveToCoprocessor2

Tyto vnitřní funkce zapisují data do koprocesorů ARM pomocí instrukcí pro přenos dat koprocesorů.

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

Parametry

value
Hodnota, která má být zapsána do koprocesoru.

koprocedura
Číslo koprocesoru v rozsahu 0 až 15.

opcode1
Operační kód pro procesor specifický pro procesor v rozsahu od 0 do 7.

crn
Číslo registru koprocesoru v rozsahu 0 až 15, který určuje první operand instrukce.

crm
Číslo registru koprocesoru v rozsahu 0 až 15, který určuje další zdrojový nebo cílový operand.

opcode2
Další operační kód pro procesor specifický pro procesor v rozsahu od 0 do 7.

Vrácená hodnota

Žádné

Poznámky

Hodnoty coprocopcode1 parametrů,, crn , crm a opcode2 vnitřních musí být konstantní výrazy, které jsou známy v době kompilace.

_MoveToCoprocessorpoužívá instrukci MCR _MoveToCoprocessor2 . používá MCR2. Parametry odpovídají bitová poleům, které jsou zakódovány přímo v pokynovém slově. Interpretace parametrů je závislá na koprocesoru. Další informace najdete v příručce k příslušnému spoluprocesoru.

_MoveToCoprocessor64

Tyto vnitřní funkce zapisují data do koprocesorů ARM pomocí instrukcí pro přenos dat koprocesorů.

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

Parametry

koprocedura
Číslo koprocesoru v rozsahu 0 až 15.

opcode1
Operační kód pro procesor specifický pro procesor v rozsahu 0 až 15.

crm
Číslo registru koprocesoru v rozsahu 0 až 15, který určuje další zdrojový nebo cílový operand.

Vrácená hodnota

Žádné

Poznámky

Hodnoty coprocopcode1 parametrů, a crm vnitřních musí být konstantní výrazy, které jsou známy v době kompilace.

_MoveFromCoprocessor64 používá instrukci MCRR. Parametry odpovídají bitová poleům, které jsou zakódovány přímo v pokynovém slově. Interpretace parametrů je závislá na koprocesoru. Další informace najdete v příručce k příslušnému spoluprocesoru.

Podpora ARM pro vnitřní objekty od ostatních architektur

Následující tabulka obsahuje seznam vnitřních objektů z jiných architektur, které jsou podporované na platformách ARM. V případě, že se chování vnitřku na ARM liší od chování v jiných hardwarových architekturách, jsou popsány další podrobnosti.

[Return to top]

Interlocked intrinsics

Interlocked intrinsics je sada vnitřních objektů, které se používají k provádění atomických operací čtení,úprav a zápisu. Některé z nich jsou společné pro všechny platformy. Jsou tady uvedené samostatně, protože jich existuje velké množství, ale vzhledem k tomu, že jejich definice jsou většinou redundantní, je jednodušší o nich obecně přemýšlet. Jejich názvy lze použít k odvození přesného chování.

Následující tabulka shrnuje podporu ARM vnitřních objektů, které nejsou vzájemně uzamčené pomocí bitových testů. Každá buňka v tabulce odpovídá názvu odvozenému připojením názvu operace v buňce nejvíce vlevo na řádku a názvu typu v horní buňce sloupce k _Interlocked . Například buňka v průniku řádku a sloupec odpovídá a Xor8 je plně _InterlockedXor8 podporována. Většina podporovaných funkcí nabízí tyto volitelné přípony: _acq_rel , a _nf . Přípona _acq označuje sémantiku "získání" a přípona označuje sémantiku _rel "vydání". Přípona nebo "žádný plot" je pro ARM jedinečná a _nf je popsána v další části.

Klíč:

• Úplné:podporuje formuláře plain, _rel , a _nf .

• Částečně: podporuje prosté formuláře, _nf a .

• Žádné:Nepodporuje se.

_nf přípony (bez plotu)

Přípona nebo "žádný plot" označuje, že se operace nechová jako žádný druh paměťové bariéry, na rozdíl od ostatních tří forem (prostých, a ), které se chovají jako nějaký druh _nf_acq_rel bariéry. Jedním z možných použití formulářů je udržování čítače statistiky, který je aktualizován více vlákny současně, ale jejichž hodnota není jinak použita při provádění _nf více vláken.

Seznam vzájemně uzamčených vnitřních objektů

[Return to top]

_interlockedbittest vnitřních objektů

Vnitřní funkce základního promyšlého bitového testu jsou společné pro všechny platformy. ARM přidává varianty , a , které mění sémantiku bariéry operace, jak je popsáno výše v tomto článku v _acq_rel části _nf _nf_acq plotu).

[Return to top]

Viz také

Vnitřní funkce kompilátoru
ARM64 – vnitřní funkce
Referenční informace k assembleru ARM
Referenční dokumentace jazyka C++