Các nhà nghiên cứu tại Viện Công nghệ Zurich vừa công bố phương thức tấn công phần cứng mang tên GPUThor. Đây là kỹ thuật Rowhammer đầu tiên thành công trong việc đánh bại cơ chế sửa lỗi phần cứng ECC (Error-Correcting Code) trên dòng GPU trung tâm dữ liệu NVIDIA RTX A6000 nhằm chiếm quyền root của máy chủ vật lý.
Bảng Thuộc Tính Kỹ Thuật:
| Tên Kỹ Thuật | GPUThor (GPU-Accelerated Rowhammer) |
| Phần Cứng Đích | NVIDIA RTX A6000 (48GB GDDR6 with ECC) |
| Cơ Chế Bẻ Khóa | Multi-Sided Aggressor Flipping bypass SECDED ECC |
| Mục Tiêu Tấn Công | Guest VM to Host Root Escape & Memory Bit Flip |
1. Nguyên Lý Tấn Công Rowhammer Trên Bộ Nhớ Đồ Họa (GDDR6)
Tấn công Rowhammer truyền thống dựa trên việc liên tục kích hoạt (activate/precharge) các hàng ô nhớ cạnh nhau trong chip DRAM ở tần số cực cao, làm rò rỉ điện tích và khiến các bit ở hàng nhớ lân cận bị lật trạng thái (0 sang 1 hoặc ngược lại). Trước đây, bộ nhớ ECC được coi là lá chắn vững chắc chống lại Rowhammer nhờ khả năng phát hiện lỗi 2 bit và tự động sửa lỗi 1 bit (SECDED).
2. Đột Phá Kỹ Thuật Của GPUThor
Nhóm nghiên cứu đã tận dụng năng lực tính toán song song khổng lồ của hàng ngàn nhân CUDA để đồng thời tấn công nhiều hàng nhớ phụ trợ (Aggressor Rows). Bằng cách điều phối chính xác thời điểm truy cập thông qua các chỉ thị CUDA PTX tùy chỉnh, GPUThor tạo ra hiện tượng Triple-Bit Flip (lật 3 bit cùng một lúc trên một từ nhớ), vượt quá khả năng tự sửa lỗi của thuật toán ECC:
// CUDA Kernel mô phỏng cơ chế kích hoạt hàng nhớ tốc độ cao trong GPUThor
__global__ void gputhor_hammer(uint32_t* __restrict__ victim_addr, int iterations) {
uint32_t* aggr1 = victim_addr - 0x1000;
uint32_t* aggr2 = victim_addr + 0x1000;
for (int i = 0; i < iterations; i++) {
// Ép buộc xóa bộ nhớ đệm L1/L2 và truy cập trực tiếp VRAM
asm volatile("ld.global.cg.u32 %0, [%1];" : "=r"(tmp) : "l"(aggr1) : "memory");
asm volatile("ld.global.cg.u32 %0, [%1];" : "=r"(tmp) : "l"(aggr2) : "memory");
}
}3. Chuỗi Khai Thác Leo Thang Đặc Quyền (Privilege Escalation)
Sau khi làm lật bit thành công trên bảng phân trang bộ nhớ của máy chủ (Page Table Entries - PTE) được lưu trong bộ nhớ chia sẻ qua PCIe, kẻ tấn công có thể ánh xạ một tiến trình người dùng không có quyền (unprivileged process) trỏ thẳng vào không gian địa chỉ bộ nhớ nhạy cảm của Linux Kernel, từ đó chiếm quyền thực thi ở cấp độ root trên máy chủ quản lý.
4. Giải Pháp Giảm Thiểu & Phòng Ngừa
- Kích hoạt Targeted Row Refresh (TRR) nâng cao: Nâng cấp Firmware BIOS/VBIOS của GPU lên phiên bản mới nhất có tích hợp thuật toán làm tươi hàng nhớ chủ động khi phát hiện tần số đọc bất thường.
- Phân lập tài nguyên GPU trong môi trường Cloud: Sử dụng công nghệ NVIDIA Multi-Instance GPU (MIG) ở cấp độ phần cứng để cô lập hoàn toàn không gian địa chỉ VRAM giữa các khách hàng thuê máy ảo.
- Giám sát cảnh báo ECC Uncorrectable Errors: Thiết lập hệ thống giám sát cảnh báo ngay lập tức khi phát hiện sự gia tăng đột biến của các sự kiện lỗi bộ nhớ không thể phục hồi trên cụm máy chủ AI/GPU.
