RGBA zu ABGR: Inline Arm Neon Asm für iOS / Xcode

Dieser Code (sehr ähnlicher Code, habe @ nicht ausprobiegena this code) Kompiliert mit Android NDK, jedoch nicht mit Xcode / armv7 + arm64 / iOS

Errors in Kommentaren:

uint32_t *src;
uint32_t *dst;

#ifdef __ARM_NEON
__asm__ volatile(
    "vld1.32 {d0, d1}, [%[src]] \n" // error: Vector register expected
    "vrev32.8 q0, q0            \n" // error: Unrecognized instruction mnemonic
    "vst1.32 {d0, d1}, [%[dst]] \n" // error: Vector register expected
    :
    : [src]"r"(src), [dst]"r"(dst)
    : "d0", "d1"
    );
#endif

Was ist los mit diesem Code?

EDIT1:

Ich habe den Code mit Intrinsics umgeschrieben:

uint8x16_t x = vreinterpretq_u8_u32(vld1q_u32(src));
uint8x16_t y = vrev32q_u8(x);
vst1q_u32(dst, vreinterpretq_u32_u8(y));

Nach dem Zerlegen erhalte ich die folgende Variante, die ich bereits ausprobiert habe:

vld1.32 {d16, d17}, [r0]!
vrev32.8    q8, q8
vst1.32 {d16, d17}, [r1]!

So sieht mein Code jetzt so aus, gibt aber genau die gleichen Fehler aus:

__asm__ volatile("vld1.32 {d0, d1}, [%0]! \n"
                 "vrev32.8 q0, q0         \n"
                 "vst1.32 {d0, d1}, [%1]! \n"
                 :
                 : "r"(src), "r"(dst)
                 : "d0", "d1"
                 );

EDIT2:

Bei der Demontage habe ich tatsächlich eine zweite Version der Funktion gefunden. Es stellt sich heraus, dass arm64 einen etwas anderen Befehlssatz verwendet. Beispielsweise verwendet die arm64-Assemblyrev32.16b v0, v0 stattdessen. Die gesamte Funktionsliste (von der ich weder Kopf noch Zahl machen kann) ist unten:

_My_Function:
cmp     w2, #0
add w9, w2, #3
csel    w8, w9, w2, lt
cmp     w9, #7
b.lo    0x3f4
asr w9, w8, #2
ldr     x8, [x0]
mov  w9, w9
lsl x9, x9, #2
ldr q0, [x8], #16
rev32.16b   v0, v0
str q0, [x1], #16
sub x9, x9, #16
cbnz    x9, 0x3e0
ret

Antworten auf die Frage(6)

Ihre Antwort auf die Frage