mirror of
https://github.com/open-goal/jak-project
synced 2026-06-10 12:55:45 -04:00
Tyler Wilding
64bcd8c030
This PR does the following: - Designs a mechanism by which arm64 instructions can be encoded and emitted - Dispatch our higher-level instruction emitting calls to either x86 or arm64 instructions depending on what the compiler is set to (defaults to x86) - Bare minimum scaffolding to get the arm64 instructions successfully executing atleast on apple silicon - Implement enough instructions to get the codetester test suite passing on arm
47 lines
860 B
C
47 lines
860 B
C
#pragma once
|
|
|
|
#include <cstdlib>
|
|
|
|
#include "common/common_types.h"
|
|
|
|
u32 crc32(const u8* data, size_t size);
|
|
|
|
#include <cstring>
|
|
|
|
#ifdef __aarch64__
|
|
#include <arm_acle.h>
|
|
// Computes CRC32C
|
|
inline u32 crc32(const u8* data, size_t size) {
|
|
u32 result = 0xffffffff;
|
|
while (size >= 4) {
|
|
result = __crc32cw(result, *reinterpret_cast<const u32*>(data));
|
|
data += 4;
|
|
size -= 4;
|
|
}
|
|
while (size) {
|
|
result = __crc32cb(result, *data);
|
|
data++;
|
|
size--;
|
|
}
|
|
return ~result;
|
|
}
|
|
#else
|
|
#include <immintrin.h>
|
|
// Computes CRC32C
|
|
inline u32 crc32(const u8* data, size_t size) {
|
|
u32 result = 0xffffffff;
|
|
while (size >= 4) {
|
|
u32 x;
|
|
memcpy(&x, data, 4);
|
|
data += 4;
|
|
size -= 4;
|
|
result = _mm_crc32_u32(result, x);
|
|
}
|
|
while (size) {
|
|
result = _mm_crc32_u8(result, *data);
|
|
data++;
|
|
size--;
|
|
}
|
|
return ~result;
|
|
}
|
|
#endif |