diff --git a/.github/workflows/qemu-riscv64.toml b/.github/workflows/qemu-riscv64.toml
new file mode 100644
index 00000000..f201c236
--- /dev/null
+++ b/.github/workflows/qemu-riscv64.toml
@@ -0,0 +1,23 @@
+args = [
+  "-nographic",
+  "-cpu",
+  "rv64",
+  "-machine",
+  "virt",
+  "-bios",
+  "default",
+  "-smp",
+  "4",
+  "-device",
+  "virtio-blk-device,drive=disk0",
+  "-drive",
+  "id=disk0,if=none,format=raw,file=${workspaceFolder}/tmp/rootfs.img",
+  "-append",
+  "root=/dev/vda rw init=/init",
+  "-m",
+  "8g",
+]
+fail_regex = []
+success_regex = ["test pass!"]
+to_bin = true
+uefi = false
\ No newline at end of file
diff --git a/.github/workflows/test-qemu.yml b/.github/workflows/test-qemu.yml
index f4e510b3..a3729e83 100644
--- a/.github/workflows/test-qemu.yml
+++ b/.github/workflows/test-qemu.yml
@@ -19,7 +19,11 @@ jobs:
           # - arch: riscv64
           #   vmconfigs: configs/vms/arceos-riscv64-qemu-smp1.toml
           #   vmconfigs_name: ArceOS
-          #   vmimage_name: qemu_arceos_riscv64
+          #   vmimage_name: qemu_riscv64_arceos
+          # - arch: riscv64
+          #   vmconfigs: configs/vms/linux-riscv64-qemu-smp1.toml
+          #   vmconfigs_name: Linux
+          #   vmimage_name: qemu_riscv64_linux
           - arch: x86_64
             vmconfigs: configs/vms/nimbos-x86_64-qemu-smp1.toml
             vmconfigs_name: NimbOS
diff --git a/Cargo.lock b/Cargo.lock
index 0b7e56a3..2868b91f 100644
--- a/Cargo.lock
+++ b/Cargo.lock
@@ -27,17 +27,6 @@ version = "0.1.1"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "0a2c929f5025d9b8a0f549b187c4d3a39671f44015ff6ccddd0b134c874b3c1a"
 
-[[package]]
-name = "abi-singleton"
-version = "0.3.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "dbdf894742ece5360a74aa8278c42e0f305aa9f7c35d43ebc9cceca105f7e434"
-dependencies = [
- "proc-macro2",
- "quote",
- "syn 2.0.111",
-]
-
 [[package]]
 name = "addr2line"
 version = "0.25.1"
@@ -112,15 +101,6 @@ dependencies = [
  "libc",
 ]
 
-[[package]]
-name = "ansi_rgb"
-version = "0.2.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "a730095eb14ee842a0f1e68504b85c8d4a19b1ef2ac2a9b4debf0ed982f9b08a"
-dependencies = [
- "rgb",
-]
-
 [[package]]
 name = "anstream"
 version = "0.6.21"
@@ -212,20 +192,6 @@ dependencies = [
  "axtask",
 ]
 
-[[package]]
-name = "arm-gic-driver"
-version = "0.14.9"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "a886a953642fbf21eb5928c49a05f021fae007219ae8cb2dafbf403dfeba974a"
-dependencies = [
- "aarch64-cpu",
- "bitflags 2.10.0",
- "enum_dispatch",
- "log",
- "rdif-intc 0.11.0",
- "tock-registers 0.9.0",
-]
-
 [[package]]
 name = "arm-gic-driver"
 version = "0.15.9"
@@ -237,7 +203,7 @@ dependencies = [
  "enum_dispatch",
  "log",
  "paste",
- "rdif-intc 0.12.1",
+ "rdif-intc",
  "tock-registers 0.9.0",
 ]
 
@@ -290,7 +256,7 @@ dependencies = [
  "axvisor_api",
  "bitmaps",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "spin 0.9.8",
  "tock-registers 0.10.1",
 ]
@@ -342,7 +308,7 @@ dependencies = [
  "cfg-if",
  "lazyinit",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "memory_set",
  "numeric-enum-macro",
  "page_table_entry",
@@ -360,7 +326,7 @@ dependencies = [
  "cfg-if",
  "kspin",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "strum 0.27.2",
 ]
 
@@ -416,7 +382,7 @@ dependencies = [
  "linkme",
  "log",
  "loongArch64",
- "memory_addr 0.4.1",
+ "memory_addr",
  "page_table_entry",
  "page_table_multiarch",
  "percpu",
@@ -439,7 +405,7 @@ dependencies = [
  "axvmconfig",
  "cfg-if",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "range-alloc",
  "spin 0.9.8",
 ]
@@ -454,7 +420,7 @@ dependencies = [
  "axerrno 0.1.2",
  "axvmconfig",
  "cfg-if",
- "memory_addr 0.4.1",
+ "memory_addr",
  "serde",
 ]
 
@@ -474,7 +440,7 @@ name = "axdriver"
 version = "0.2.0"
 source = "git+https://github.com/arceos-org/arceos.git?tag=dev-251216#16096568f5ae6ad2d687eff2927a4cb69cef8133"
 dependencies = [
- "arm-gic-driver 0.15.9",
+ "arm-gic-driver",
  "axalloc",
  "axconfig",
  "axdriver_base 0.1.2 (git+https://github.com/arceos-org/axdriver_crates.git?tag=dev-v01)",
@@ -491,10 +457,10 @@ dependencies = [
  "crate_interface",
  "dma-api 0.5.2",
  "log",
- "memory_addr 0.4.1",
- "rdif-block 0.6.2",
- "rdif-intc 0.12.1",
- "rdrive 0.18.11",
+ "memory_addr",
+ "rdif-block",
+ "rdif-intc",
+ "rdrive",
  "smallvec",
  "spin 0.10.0",
 ]
@@ -615,7 +581,7 @@ dependencies = [
  "fatfs",
  "lazyinit",
  "log",
- "rsext4 0.1.0 (git+https://github.com/Dirinkbottle/rsext4.git?tag=dev-251222)",
+ "rsext4",
  "spin 0.9.8",
 ]
 
@@ -661,7 +627,7 @@ dependencies = [
  "lazyinit",
  "linkme",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "page_table_multiarch",
  "percpu",
 ]
@@ -703,7 +669,7 @@ version = "0.2.0"
 source = "git+https://github.com/arceos-hypervisor/axklib.git#7c0fc0588f978f7d75bb94f4e07477776ed37887"
 dependencies = [
  "axerrno 0.1.2",
- "memory_addr 0.4.1",
+ "memory_addr",
  "trait-ffi",
 ]
 
@@ -730,7 +696,7 @@ dependencies = [
  "kspin",
  "lazyinit",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "memory_set",
 ]
 
@@ -763,7 +729,7 @@ dependencies = [
  "crate_interface",
  "handler_table",
  "kspin",
- "memory_addr 0.4.1",
+ "memory_addr",
  "percpu",
 ]
 
@@ -775,7 +741,7 @@ dependencies = [
  "aarch64-cpu",
  "aarch64-cpu-ext",
  "any-uart",
- "arm-gic-driver 0.15.9",
+ "arm-gic-driver",
  "axconfig-macros",
  "axcpu",
  "axplat",
@@ -783,12 +749,12 @@ dependencies = [
  "heapless 0.8.0",
  "lazyinit",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "page_table_entry",
  "paste",
  "percpu",
- "rdif-intc 0.12.1",
- "rdrive 0.18.11",
+ "rdif-intc",
+ "rdrive",
  "serde",
  "somehal",
  "spin 0.10.0",
@@ -801,7 +767,7 @@ version = "0.3.0"
 source = "git+https://github.com/arceos-org/axplat_crates.git?tag=dev-v03#0df0713b1c20eafaeebdc6b0e194b2985e857949"
 dependencies = [
  "aarch64-cpu",
- "arm-gic-driver 0.15.9",
+ "arm-gic-driver",
  "arm_pl011",
  "arm_pl031",
  "axcpu",
@@ -1008,7 +974,7 @@ dependencies = [
  "kspin",
  "lazyinit",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "percpu",
 ]
 
@@ -1072,7 +1038,7 @@ dependencies = [
  "axaddrspace",
  "axerrno 0.1.2",
  "axvisor_api",
- "memory_addr 0.4.1",
+ "memory_addr",
  "percpu",
 ]
 
@@ -1082,7 +1048,7 @@ version = "0.0.0"
 dependencies = [
  "aarch64-cpu-ext",
  "anyhow",
- "arm-gic-driver 0.15.9",
+ "arm-gic-driver",
  "axaddrspace",
  "axconfig",
  "axdevice",
@@ -1107,14 +1073,14 @@ dependencies = [
  "lazy_static",
  "lazyinit",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "page_table_entry",
  "page_table_multiarch",
  "percpu",
  "prettyplease",
  "quote",
- "rdif-intc 0.12.1",
- "rdrive 0.18.11",
+ "rdif-intc",
+ "rdrive",
  "spin 0.9.8",
  "syn 2.0.111",
  "timer_list",
@@ -1131,7 +1097,7 @@ dependencies = [
  "axaddrspace",
  "axvisor_api_proc",
  "crate_interface",
- "memory_addr 0.4.1",
+ "memory_addr",
 ]
 
 [[package]]
@@ -1162,7 +1128,7 @@ dependencies = [
  "cfg-if",
  "cpumask",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "page_table_entry",
  "page_table_multiarch",
  "percpu",
@@ -1208,19 +1174,6 @@ version = "1.0.0"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "f8fe8f5a8a398345e52358e18ff07cc17a568fbca5c6f73873d3a62056309603"
 
-[[package]]
-name = "bare-test"
-version = "0.4.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "f7dfcf95987c500af4665d8a18adbc5e7d3177a2537964f48002b88e28fb055e"
-dependencies = [
- "bare-test-macros",
- "log",
- "sparreal-kernel",
- "sparreal-macros 0.9.3",
- "sparreal-rt",
-]
-
 [[package]]
 name = "bare-test-macros"
 version = "0.2.0"
@@ -1264,26 +1217,6 @@ dependencies = [
  "tar",
 ]
 
-[[package]]
-name = "bindgen"
-version = "0.71.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "5f58bf3d7db68cfbac37cfc485a8d711e87e064c3d0fe0435b92f7a407f9d6b3"
-dependencies = [
- "bitflags 2.10.0",
- "cexpr",
- "clang-sys",
- "itertools 0.13.0",
- "log",
- "prettyplease",
- "proc-macro2",
- "quote",
- "regex",
- "rustc-hash",
- "shlex",
- "syn 2.0.111",
-]
-
 [[package]]
 name = "bit"
 version = "0.1.1"
@@ -1367,15 +1300,6 @@ dependencies = [
  "syn 2.0.111",
 ]
 
-[[package]]
-name = "buddy_system_allocator"
-version = "0.11.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "a1a0108968a3a2dab95b089c0fc3f1afa7759aa5ebe6f1d86d206d6f7ba726eb"
-dependencies = [
- "spin 0.9.8",
-]
-
 [[package]]
 name = "bumpalo"
 version = "3.19.1"
@@ -1541,15 +1465,6 @@ dependencies = [
  "shlex",
 ]
 
-[[package]]
-name = "cexpr"
-version = "0.6.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "6fac387a98bb7c37292057cffc56d62ecb629900026402633ae9160df93a8766"
-dependencies = [
- "nom",
-]
-
 [[package]]
 name = "cfg-if"
 version = "1.0.4"
@@ -1575,17 +1490,6 @@ dependencies = [
  "windows-link",
 ]
 
-[[package]]
-name = "clang-sys"
-version = "1.8.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "0b023947811758c97c59bf9d1c188fd619ad4718dcaa767947df1cadb14f39f4"
-dependencies = [
- "glob",
- "libc",
- "libloading",
-]
-
 [[package]]
 name = "clap"
 version = "4.5.53"
@@ -1866,16 +1770,6 @@ dependencies = [
  "typenum",
 ]
 
-[[package]]
-name = "cstr_core"
-version = "0.2.6"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "dd98742e4fdca832d40cab219dc2e3048de17d873248f83f17df47c1bea70956"
-dependencies = [
- "cty",
- "memchr",
-]
-
 [[package]]
 name = "ctor_bare"
 version = "0.2.1"
@@ -1896,12 +1790,6 @@ dependencies = [
  "syn 2.0.111",
 ]
 
-[[package]]
-name = "cty"
-version = "0.2.2"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "b365fabc795046672053e29c954733ec3b05e4be654ab130fe8f1f94d7051f35"
-
 [[package]]
 name = "cursive"
 version = "0.21.1"
@@ -2163,10 +2051,10 @@ version = "0.1.0"
 dependencies = [
  "axklib",
  "log",
- "phytium-mci 0.1.0 (git+https://github.com/YanQD/phytium-mci.git?rev=99c9ee5)",
- "rdif-block 0.6.2",
+ "phytium-mci",
+ "rdif-block",
  "rdif-clk",
- "rdrive 0.18.11",
+ "rdrive",
  "rk3568_clk",
  "rk3588-clk",
  "rockchip-pm",
@@ -2616,12 +2504,6 @@ version = "0.32.3"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "e629b9b98ef3dd8afe6ca2bd0f89306cec16d43d907889945bc5d6687f2f13c7"
 
-[[package]]
-name = "glob"
-version = "0.3.3"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "0cc23270f6e1808e30a928bdc84dea0b9b4136a8bc82338574f23baf47bbd280"
-
 [[package]]
 name = "h2"
 version = "0.3.27"
@@ -3150,15 +3032,6 @@ version = "1.70.2"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "a6cb138bb79a146c1bd460005623e142ef0181e3d0219cb493e02f7d08a35695"
 
-[[package]]
-name = "itertools"
-version = "0.9.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "284f18f85651fe11e8a991b2adb42cb078325c996ed026d994719efcfca1d54b"
-dependencies = [
- "either",
-]
-
 [[package]]
 name = "itertools"
 version = "0.13.0"
@@ -3231,18 +3104,6 @@ dependencies = [
  "wasm-bindgen",
 ]
 
-[[package]]
-name = "kasm-aarch64"
-version = "0.1.3"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "e484b7a4686e2750fae1b4c4b750e14f1522eb303288d9d2723a955c2a41b7d7"
-dependencies = [
- "darling 0.20.11",
- "proc-macro2",
- "quote",
- "syn 2.0.111",
-]
-
 [[package]]
 name = "kasm-aarch64"
 version = "0.2.0"
@@ -3337,16 +3198,6 @@ version = "0.2.178"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "37c93d8daa9d8a012fd8ab92f088405fb202ea0b6ab73ee2482ae66af4f42091"
 
-[[package]]
-name = "libloading"
-version = "0.8.9"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "d7c4b02199fee7c5d21a5ae7d8cfa79a6ef5bb2fc834d6e9058e89c825efdc55"
-dependencies = [
- "cfg-if",
- "windows-link",
-]
-
 [[package]]
 name = "libredox"
 version = "0.1.11"
@@ -3479,15 +3330,6 @@ version = "0.1.2"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "112b39cec0b298b6c1999fee3e31427f74f676e4cb9879ed1a121b43661a4154"
 
-[[package]]
-name = "lwext4_rust"
-version = "0.2.0"
-dependencies = [
- "bindgen",
- "log",
- "printf-compat",
-]
-
 [[package]]
 name = "lzma-rs"
 version = "0.3.0"
@@ -3546,12 +3388,6 @@ dependencies = [
  "autocfg",
 ]
 
-[[package]]
-name = "memory_addr"
-version = "0.3.2"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "5438b8df0f13e16e1f46140de247695a95952a5a4479e47197a8711bf1063373"
-
 [[package]]
 name = "memory_addr"
 version = "0.4.1"
@@ -3565,7 +3401,7 @@ source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "50a49ecd4114cf87f7e442ec5dd03bd590e7094541f987057310dbb32a6341ad"
 dependencies = [
  "axerrno 0.1.2",
- "memory_addr 0.4.1",
+ "memory_addr",
 ]
 
 [[package]]
@@ -3584,12 +3420,6 @@ dependencies = [
  "unicase",
 ]
 
-[[package]]
-name = "minimal-lexical"
-version = "0.2.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "68354c5c6bd36d73ff3feceb05efa59b6acb7626617f4962be322a825e61f79a"
-
 [[package]]
 name = "miniz_oxide"
 version = "0.8.9"
@@ -3667,16 +3497,6 @@ dependencies = [
  "libc",
 ]
 
-[[package]]
-name = "nom"
-version = "7.1.3"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "d273983c5a657a70a3e8f2a01329822f3b8c8172b73826411a55751e404a0a4a"
-dependencies = [
- "memchr",
- "minimal-lexical",
-]
-
 [[package]]
 name = "nop"
 version = "0.1.0"
@@ -3882,28 +3702,6 @@ dependencies = [
  "ureq",
 ]
 
-[[package]]
-name = "page-table-arm"
-version = "0.1.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "2ce2c42338660c47a35e7b2940dcccbe6612a4a0aa0485ecdf4e23aa8a2a1158"
-dependencies = [
- "aarch64-cpu",
- "bitflags 2.10.0",
- "log",
-]
-
-[[package]]
-name = "page-table-generic"
-version = "0.5.3"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "827063f64bbad7b7655092b0f98824ffbe85e89646388eb4dad1e3d797056a2f"
-dependencies = [
- "bitflags 2.10.0",
- "log",
- "thiserror 2.0.17",
-]
-
 [[package]]
 name = "page-table-generic"
 version = "0.6.1"
@@ -3924,7 +3722,7 @@ checksum = "dda9891ec368fda90e4b2cc36592b4881073e25a339fe7e3eddd811f0cf6bf18"
 dependencies = [
  "aarch64-cpu",
  "bitflags 2.10.0",
- "memory_addr 0.4.1",
+ "memory_addr",
  "x86_64",
 ]
 
@@ -3935,7 +3733,7 @@ source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "9fa11a21844255e14aa6688ef0eafb058d7be19338633024fb59417f1bfb07f8"
 dependencies = [
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "page_table_entry",
  "riscv",
  "x86",
@@ -3970,12 +3768,6 @@ version = "1.0.15"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "57c0d7b74b563b49d38dae00a0c37d4d6de9b432382b2892f0574ddcae73fd0a"
 
-[[package]]
-name = "pasts"
-version = "0.14.3"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "efcd36303871fb977a47dabc9af736c75c492bb32a92fa26262b2741531e97ce"
-
 [[package]]
 name = "pci_types"
 version = "0.10.0"
@@ -3986,19 +3778,6 @@ dependencies = [
  "bitflags 2.10.0",
 ]
 
-[[package]]
-name = "pcie"
-version = "0.2.7"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "63e45cda4b8ef9f2a8dae7cf5b58c11b41d35fbe62a4d9693fd2d143225fbf44"
-dependencies = [
- "bit_field",
- "bitflags 2.10.0",
- "log",
- "pci_types",
- "sparreal-macros 0.0.5",
-]
-
 [[package]]
 name = "pcie"
 version = "0.4.5"
@@ -4043,26 +3822,6 @@ dependencies = [
  "syn 2.0.111",
 ]
 
-[[package]]
-name = "phytium-mci"
-version = "0.1.0"
-dependencies = [
- "bare-test",
- "bare-test-macros",
- "bitflags 2.10.0",
- "byte-unit",
- "bytemuck",
- "dma-api 0.2.2",
- "lazy_static",
- "log",
- "nb",
- "pcie 0.2.7",
- "rlsf",
- "spin 0.10.0",
- "spin_on",
- "tock-registers 0.9.0",
-]
-
 [[package]]
 name = "phytium-mci"
 version = "0.1.0"
@@ -4080,33 +3839,6 @@ dependencies = [
  "tock-registers 0.9.0",
 ]
 
-[[package]]
-name = "pie-boot"
-version = "0.2.20"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "524d0fc5cd834d2179d8a88cde327b0e168dd6aedf30ce1832467a924a35594f"
-dependencies = [
- "aarch64-cpu",
- "aarch64-cpu-ext",
- "bindeps-simple",
- "fdt-parser",
- "heapless 0.8.0",
- "kasm-aarch64 0.1.3",
- "kdef-pgtable",
- "pie-boot-if 0.6.0",
- "pie-boot-loader-aarch64 0.1.27",
- "pie-boot-macros",
-]
-
-[[package]]
-name = "pie-boot-if"
-version = "0.6.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "c00af8d4efee0eee91ead95b34c50c067163dc4c90b874b1cc4caa671eb1d85b"
-dependencies = [
- "heapless 0.8.0",
-]
-
 [[package]]
 name = "pie-boot-if"
 version = "0.8.0"
@@ -4116,30 +3848,6 @@ dependencies = [
  "heapless 0.8.0",
 ]
 
-[[package]]
-name = "pie-boot-loader-aarch64"
-version = "0.1.27"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "e4ee18ed1de7f55f318f01803bf7dc353ef492db71a2005fa3af36f116f25d28"
-dependencies = [
- "aarch64-cpu",
- "aarch64-cpu-ext",
- "any-uart",
- "bitflags 2.10.0",
- "fdt-parser",
- "kasm-aarch64 0.1.3",
- "kdef-pgtable",
- "log",
- "num-align",
- "page-table-generic 0.6.1",
- "pie-boot-if 0.6.0",
- "prettyplease",
- "quote",
- "spin 0.10.0",
- "syn 2.0.111",
- "thiserror 2.0.17",
-]
-
 [[package]]
 name = "pie-boot-loader-aarch64"
 version = "0.3.3"
@@ -4151,12 +3859,12 @@ dependencies = [
  "any-uart",
  "bitflags 2.10.0",
  "fdt-parser",
- "kasm-aarch64 0.2.0",
+ "kasm-aarch64",
  "kdef-pgtable",
  "log",
  "num-align",
- "page-table-generic 0.6.1",
- "pie-boot-if 0.8.0",
+ "page-table-generic",
+ "pie-boot-if",
  "prettyplease",
  "quote",
  "spin 0.10.0",
@@ -4243,18 +3951,6 @@ dependencies = [
  "syn 2.0.111",
 ]
 
-[[package]]
-name = "printf-compat"
-version = "0.1.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "3b002af28ffe3d3d67202ae717810a28125a494d5396debc43de01ee136ac404"
-dependencies = [
- "bitflags 1.3.2",
- "cstr_core",
- "cty",
- "itertools 0.9.0",
-]
-
 [[package]]
 name = "proc-macro-crate"
 version = "3.4.0"
@@ -4467,7 +4163,7 @@ dependencies = [
  "crossterm 0.28.1",
  "indoc",
  "instability",
- "itertools 0.13.0",
+ "itertools",
  "lru",
  "paste",
  "strum 0.26.3",
@@ -4494,18 +4190,6 @@ dependencies = [
  "bitflags 2.10.0",
 ]
 
-[[package]]
-name = "rdif-base"
-version = "0.6.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "b6953f438bbbdf58e55513c31e70fa0f85daba2927e8a59130a04608141bb552"
-dependencies = [
- "as-any",
- "async-trait",
- "rdif-def",
- "thiserror 2.0.17",
-]
-
 [[package]]
 name = "rdif-base"
 version = "0.7.0"
@@ -4519,16 +4203,6 @@ dependencies = [
  "thiserror 2.0.17",
 ]
 
-[[package]]
-name = "rdif-block"
-version = "0.5.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "c7b8e19dc3cb6cd7241085a9560a91d4346edbc525bcbfc3c86e5eeb11559c19"
-dependencies = [
- "cfg-if",
- "rdif-base 0.6.0",
-]
-
 [[package]]
 name = "rdif-block"
 version = "0.6.2"
@@ -4538,7 +4212,7 @@ dependencies = [
  "cfg-if",
  "dma-api 0.5.2",
  "futures",
- "rdif-base 0.7.0",
+ "rdif-base",
  "spin_on",
  "thiserror 2.0.17",
 ]
@@ -4549,7 +4223,7 @@ version = "0.4.2"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "b9af012204e25d45735aa141b475c411b833b4f4bc580924905745d4afbbf606"
 dependencies = [
- "rdif-base 0.7.0",
+ "rdif-base",
 ]
 
 [[package]]
@@ -4561,17 +4235,6 @@ dependencies = [
  "thiserror 2.0.17",
 ]
 
-[[package]]
-name = "rdif-intc"
-version = "0.11.0"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "a4e7622f78dc9b40958500119553f3c15b9bb9829002d87d0f4b114ebe302a40"
-dependencies = [
- "cfg-if",
- "rdif-base 0.6.0",
- "thiserror 2.0.17",
-]
-
 [[package]]
 name = "rdif-intc"
 version = "0.12.1"
@@ -4579,7 +4242,7 @@ source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "170ec813e6cf4d1e5fa53fa8fed0fadc7aaab96683d4f1d44c602a6109931eb4"
 dependencies = [
  "cfg-if",
- "rdif-base 0.7.0",
+ "rdif-base",
  "thiserror 2.0.17",
 ]
 
@@ -4590,59 +4253,7 @@ source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "60c6e8dea6d432b2c03bc3f4238dc59a276aacac6f688a937351e7a313918738"
 dependencies = [
  "pci_types",
- "rdif-base 0.7.0",
- "thiserror 2.0.17",
-]
-
-[[package]]
-name = "rdif-power"
-version = "0.6.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "c7b6eefca0d1b44a5bef1e934d8ab2c8e00e19dd3d9e071855c0933637ee17a0"
-dependencies = [
- "rdif-base 0.7.0",
-]
-
-[[package]]
-name = "rdif-serial"
-version = "0.4.2"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "673854a0c554806da63f0836c95b34b08956a143ff15e327644cbd07a8e0df31"
-dependencies = [
- "futures",
- "rdif-base 0.7.0",
- "spin_on",
- "thiserror 2.0.17",
-]
-
-[[package]]
-name = "rdif-systick"
-version = "0.5.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "e11da4f362ab6cdcdee9d8e795faabd0f15e04167cb17939fd3aca19c2ef3421"
-dependencies = [
- "rdif-base 0.7.0",
-]
-
-[[package]]
-name = "rdrive"
-version = "0.15.3"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "72ce47e5a3d10943dfdb8c31dcca7a91c353ea43f4ac2eb72c92462e83a2baa4"
-dependencies = [
- "enum_dispatch",
- "fdt-parser",
- "log",
- "paste",
- "rdif-base 0.6.0",
- "rdif-block 0.5.0",
- "rdif-clk",
- "rdif-intc 0.11.0",
- "rdif-power",
- "rdif-serial",
- "rdif-systick",
- "rdrive-macros",
- "spin 0.10.0",
+ "rdif-base",
  "thiserror 2.0.17",
 ]
 
@@ -4655,25 +4266,14 @@ dependencies = [
  "fdt-parser",
  "log",
  "paste",
- "pcie 0.4.5",
- "rdif-base 0.7.0",
+ "pcie",
+ "rdif-base",
  "rdif-pcie",
  "rdrive-macros",
  "spin 0.10.0",
  "thiserror 2.0.17",
 ]
 
-[[package]]
-name = "rdrive-macro-utils"
-version = "0.2.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "977fcecf5b5fe8d7189d497d8754d27a4ffaedeac904cce1b7ea7bdfb5280934"
-dependencies = [
- "proc-macro2",
- "quote",
- "syn 2.0.111",
-]
-
 [[package]]
 name = "rdrive-macros"
 version = "0.4.1"
@@ -4863,15 +4463,6 @@ dependencies = [
  "webpki-roots",
 ]
 
-[[package]]
-name = "rgb"
-version = "0.8.52"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "0c6a884d2998352bb4daf0183589aec883f16a6da1f4dde84d8e2e9a5409a1ce"
-dependencies = [
- "bytemuck",
-]
-
 [[package]]
 name = "ring"
 version = "0.17.14"
@@ -4960,7 +4551,7 @@ dependencies = [
  "crate_interface",
  "log",
  "memoffset",
- "memory_addr 0.4.1",
+ "memory_addr",
  "page_table_entry",
  "riscv",
  "riscv-decode",
@@ -5043,19 +4634,10 @@ dependencies = [
  "dma-api 0.5.2",
  "log",
  "mbarrier",
- "rdif-base 0.7.0",
+ "rdif-base",
  "tock-registers 0.10.1",
 ]
 
-[[package]]
-name = "rsext4"
-version = "0.1.0"
-dependencies = [
- "bitflags 2.10.0",
- "lazy_static",
- "log",
-]
-
 [[package]]
 name = "rsext4"
 version = "0.1.0"
@@ -5287,7 +4869,7 @@ dependencies = [
  "kspin",
  "log",
  "paste",
- "smccc 0.2.2",
+ "smccc",
  "spin 0.10.0",
 ]
 
@@ -5560,12 +5142,6 @@ version = "1.15.1"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "67b1b7a3b5fe4f1376887184045fcf45c69e92af734b7aaddc05fb777b6fbd03"
 
-[[package]]
-name = "smccc"
-version = "0.1.1"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "617d17f088ec733e5a6b86da6ce4cce1414e6e856d6061c16dda51cceae6f68c"
-
 [[package]]
 name = "smccc"
 version = "0.2.2"
@@ -5622,100 +5198,22 @@ dependencies = [
  "fdt-parser",
  "futures",
  "heapless 0.8.0",
- "kasm-aarch64 0.2.0",
+ "kasm-aarch64",
  "kdef-pgtable",
  "log",
  "num-align",
- "page-table-generic 0.6.1",
- "pie-boot-if 0.8.0",
- "pie-boot-loader-aarch64 0.3.3",
+ "page-table-generic",
+ "pie-boot-if",
+ "pie-boot-loader-aarch64",
  "pie-boot-macros",
  "release-dep",
  "serde",
- "smccc 0.2.2",
+ "smccc",
  "spin 0.10.0",
  "toml 0.9.10+spec-1.1.0",
  "url",
 ]
 
-[[package]]
-name = "sparreal-kernel"
-version = "0.9.4"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "b182a508314f1560ce8f94090f8c0990640bd849fab49e307ccafe2b51e67da9"
-dependencies = [
- "ansi_rgb",
- "anyhow",
- "arrayvec",
- "buddy_system_allocator",
- "byte-unit",
- "dma-api 0.3.1",
- "fdt-parser",
- "lazy_static",
- "lock_api",
- "log",
- "memory_addr 0.3.2",
- "page-table-generic 0.5.3",
- "pasts",
- "rdrive 0.15.3",
- "rgb",
- "sparreal-macros 0.9.3",
- "spin 0.9.8",
- "thiserror 2.0.17",
-]
-
-[[package]]
-name = "sparreal-macros"
-version = "0.0.5"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "f686073b67b2427c9243bddc10ea0a6a5300ab5354a8ee884d9126854b0abab7"
-dependencies = [
- "proc-macro2",
- "quote",
- "syn 2.0.111",
-]
-
-[[package]]
-name = "sparreal-macros"
-version = "0.9.3"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "7c39b68430130f1c7587eb41f512dd1f6e48bc22a3e1dc11a69dc1b8294cdc90"
-dependencies = [
- "abi-singleton",
- "darling 0.20.11",
- "proc-macro2",
- "quote",
- "rdrive-macro-utils",
- "syn 2.0.111",
-]
-
-[[package]]
-name = "sparreal-rt"
-version = "0.9.8"
-source = "registry+https://github.com/rust-lang/crates.io-index"
-checksum = "f9da6adb0285c99f180e9746ebbadcf4886b1b009904f6f9ab5be155ae1325a7"
-dependencies = [
- "aarch64-cpu",
- "aarch64-cpu-ext",
- "ansi_rgb",
- "any-uart",
- "arm-gic-driver 0.14.9",
- "arrayvec",
- "buddy_system_allocator",
- "fdt-parser",
- "log",
- "memory_addr 0.3.2",
- "numeric-enum-macro",
- "page-table-arm",
- "page-table-generic 0.5.3",
- "pie-boot",
- "rgb",
- "smccc 0.1.1",
- "sparreal-kernel",
- "sparreal-macros 0.9.3",
- "spin 0.9.8",
-]
-
 [[package]]
 name = "spin"
 version = "0.9.8"
@@ -6391,7 +5889,7 @@ version = "1.1.0"
 source = "registry+https://github.com/rust-lang/crates.io-index"
 checksum = "b3644627a5af5fa321c95b9b235a72fd24cd29c648c2c379431e6628655627bf"
 dependencies = [
- "itertools 0.13.0",
+ "itertools",
  "unicode-segmentation",
  "unicode-width 0.1.14",
 ]
@@ -7082,7 +6580,7 @@ dependencies = [
  "cfg-if",
  "crate_interface",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "numeric-enum-macro",
  "page_table_entry",
  "paste",
@@ -7105,7 +6603,7 @@ dependencies = [
  "axvisor_api",
  "bit",
  "log",
- "memory_addr 0.4.1",
+ "memory_addr",
  "paste",
  "tock-registers 0.10.1",
 ]
diff --git a/configs/board/qemu-riscv64.toml b/configs/board/qemu-riscv64.toml
new file mode 100644
index 00000000..5e3d701b
--- /dev/null
+++ b/configs/board/qemu-riscv64.toml
@@ -0,0 +1,12 @@
+cargo_args = []
+features = [
+    "axstd/myplat",
+    "ept-level-4",
+    "axstd/bus-mmio",
+    # "fs",
+]
+log = "Info"
+target = "riscv64gc-unknown-none-elf"
+to_bin = true
+vm_configs = []
+smp = 4
\ No newline at end of file
diff --git a/configs/vms/arceos-riscv64-qemu-smp1.toml b/configs/vms/arceos-riscv64-qemu-smp1.toml
new file mode 100644
index 00000000..56ba0d1b
--- /dev/null
+++ b/configs/vms/arceos-riscv64-qemu-smp1.toml
@@ -0,0 +1,72 @@
+# Vm base info configs
+#
+[base]
+# Guest vm id.
+id = 1
+# Guest vm name.
+name = "arceos-qemu"
+# Virtualization type.
+vm_type = 1
+# The number of virtual CPUs.
+cpu_num = 1
+# Guest vm physical cpu ids.
+phys_cpu_ids = [0]
+
+#
+# Vm kernel configs
+#
+[kernel]
+# The entry point of the kernel image.
+entry_point = 0x8020_0000
+# The location of image: "memory" | "fs".
+# load from memory.
+image_location = "fs"
+# The file path of the kernel image.
+kernel_path = "/guest/images/qemu_riscv64_linux/qemu-riscv64"
+# The load address of the kernel image.
+kernel_load_addr = 0x8020_0000
+# The file path of the device tree blob (DTB).
+#dtb_path = "path/aarch64-qemu-gicv3.dtb"
+# The load address of the device tree blob (DTB).
+dtb_load_addr = 0x8220_0000
+
+## The file path of the ramdisk image.
+# ramdisk_path = ""
+## The load address of the ramdisk image.
+# ramdisk_load_addr = 0
+## The path of the disk image.
+# disk_path = "disk.img"
+
+# Memory regions with format (`base_paddr`, `size`, `flags`, `map_type`).
+# For `map_type`, 0 means `MAP_ALLOC`, 1 means `MAP_IDENTICAL`.
+memory_regions = [
+  [0x8000_0000, 0x800_0000, 0x7, 0], # System RAM 1G MAP_ALLOC
+]
+
+#
+# Device specifications
+#
+[devices]
+# Pass-through devices.
+passthrough_devices = [
+]
+
+# Passthrough addresses.
+# Base-GPA  Length.
+passthrough_addresses = [
+    #[0x28041000, 0x100_0000]
+]
+
+# Devices that are not desired to be passed through to the guest
+excluded_devices = [
+]
+
+# Emu_devices.
+# Name Base-Ipa Ipa_len Alloc-Irq Emu-Type EmuConfig.
+emu_devices = [
+  # ["gppt-gicd", 0x0800_0000, 0x1_0000, 0, 0x21, []],
+  # ["gppt-gicr", 0x080a_0000, 0x2_0000, 0, 0x20, [1, 0x2_0000, 0]], # 1 vcpu, stride 0x20000, starts with pcpu 0
+  # ["gppt-gits", 0x0808_0000, 0x2_0000, 0, 0x22, [0x0808_0000]], # host_gits_base
+]
+
+interrupt_mode = "passthrough"
diff --git a/configs/vms/linux-riscv64-qemu-smp1.dts b/configs/vms/linux-riscv64-qemu-smp1.dts
new file mode 100644
index 00000000..ea2849b6
--- /dev/null
+++ b/configs/vms/linux-riscv64-qemu-smp1.dts
@@ -0,0 +1,132 @@
+/dts-v1/;
+
+/ {
+	#address-cells = <0x02>;
+	#size-cells = <0x02>;
+	compatible = "riscv-virtio";
+	model = "riscv-virtio,qemu";
+
+	memory@90000000 {
+		device_type = "memory";
+		reg = <0x00 0x90000000 0x00 0x40000000>;
+	};
+
+	cpus {
+		#address-cells = <0x01>;
+		#size-cells = <0x00>;
+		timebase-frequency = <0x989680>;
+
+		cpu@0 {
+			phandle = <0x07>;
+			device_type = "cpu";
+			reg = <0x00>;
+			status = "okay";
+			compatible = "riscv";
+			riscv,cbop-block-size = <0x40>;
+			riscv,cboz-block-size = <0x40>;
+			riscv,cbom-block-size = <0x40>;
+			riscv,isa-extensions = "i", "m", "a", "f", "d", "c";
+			riscv,isa-base = "rv64i";
+			riscv,isa = "rv64imafdc";
+			mmu-type = "riscv,sv39";
+
+			interrupt-controller {
+				#interrupt-cells = <0x01>;
+				interrupt-controller;
+				compatible = "riscv,cpu-intc";
+				phandle = <0x08>;
+			};
+		};
+	};
+
+	aliases {
+		serial0 = "/soc/serial@10000000";
+	};
+
+	chosen {
+		bootargs = "earlycon=sbi console=ttyS0,115200 init=/init root=/dev/vda rw";
+		stdout-path = "/soc/serial@10000000";
+	};
+
+	soc {
+		#address-cells = <0x02>;
+		#size-cells = <0x02>;
+		compatible = "simple-bus";
+		ranges;
+
+		serial@10000000 {
+			interrupts = <0x0a>;
+			interrupt-parent = <0x09>;
+			clock-frequency = "", "8@";
+			reg = <0x00 0x10000000 0x00 0x100>;
+			compatible = "ns16550a";
+		};
+
+		plic@c000000 {
+			phandle = <0x09>;
+			riscv,ndev = <0x5f>;
+			reg = <0x00 0xc000000 0x00 0x600000>;
+			interrupts-extended = <0x08 0x0b 0x08 0x09>;
+			interrupt-controller;
+			compatible = "sifive,plic-1.0.0", "riscv,plic0";
+			#address-cells = <0x00>;
+			#interrupt-cells = <0x01>;
+		};
+
+		virtio_mmio@10008000 {
+			interrupts = <0x08>;
+			interrupt-parent = <0x09>;
+			reg = <0x00 0x10008000 0x00 0x1000>;
+			compatible = "virtio,mmio";
+		};
+
+		virtio_mmio@10007000 {
+			interrupts = <0x07>;
+			interrupt-parent = <0x09>;
+			reg = <0x00 0x10007000 0x00 0x1000>;
+			compatible = "virtio,mmio";
+		};
+
+		virtio_mmio@10006000 {
+			interrupts = <0x06>;
+			interrupt-parent = <0x09>;
+			reg = <0x00 0x10006000 0x00 0x1000>;
+			compatible = "virtio,mmio";
+		};
+
+		virtio_mmio@10005000 {
+			interrupts = <0x05>;
+			interrupt-parent = <0x09>;
+			reg = <0x00 0x10005000 0x00 0x1000>;
+			compatible = "virtio,mmio";
+		};
+
+		virtio_mmio@10004000 {
+			interrupts = <0x04>;
+			interrupt-parent = <0x09>;
+			reg = <0x00 0x10004000 0x00 0x1000>;
+			compatible = "virtio,mmio";
+		};
+
+		virtio_mmio@10003000 {
+			interrupts = <0x03>;
+			interrupt-parent = <0x09>;
+			reg = <0x00 0x10003000 0x00 0x1000>;
+			compatible = "virtio,mmio";
+		};
+
+		virtio_mmio@10002000 {
+			interrupts = <0x02>;
+			interrupt-parent = <0x09>;
+			reg = <0x00 0x10002000 0x00 0x1000>;
+			compatible = "virtio,mmio";
+		};
+
+		virtio_mmio@10001000 {
+			interrupts = <0x01>;
+			interrupt-parent = <0x09>;
+			reg = <0x00 0x10001000 0x00 0x1000>;
+			compatible = "virtio,mmio";
+		};
+	};
+};
diff --git a/configs/vms/linux-riscv64-qemu-smp1.toml b/configs/vms/linux-riscv64-qemu-smp1.toml
new file mode 100644
index 00000000..084807d3
--- /dev/null
+++ b/configs/vms/linux-riscv64-qemu-smp1.toml
@@ -0,0 +1,67 @@
+# Vm base info configs
+#
+[base]
+# Guest vm id.
+id = 1
+# Guest vm name.
+name = "linux-qemu"
+# Virtualization type.
+vm_type = 1
+# The number of virtual CPUs.
+cpu_num = 1
+# Guest vm physical cpu sets.
+phys_cpu_ids = [0]
+
+#
+# Vm kernel configs
+#
+[kernel]
+# The entry point of the kernel image.
+entry_point = 0x9000_0000
+# The location of image: "memory" | "fs".
+# load from memory.
+image_location = "fs"
+# The file path of the kernel image.
+# kernel_path = "linux-6.6.62.bin"
+kernel_path = "/guest/images/qemu_riscv64_linux/qemu-riscv64"
+# The load address of the kernel image.
+kernel_load_addr = 0x9000_0000
+# The file path of the device tree blob (DTB).
+dtb_path = "/guest/images/linux-riscv64-qemu-smp1.dtb"
+# The load address of the device tree blob (DTB).
+dtb_load_addr = 0x9200_0000
+
+# Memory regions with format (`base_paddr`, `size`, `flags`, `map_type`).
+# For `map_type`, 0 means `MAP_ALLOC`, 1 means `MAP_IDENTICAL`.
+memory_regions = [
+    [0x9000_0000, 0x4000_0000, 0x7, 2], # System RAM 1G MAP_IDENTICAL
+]
+
+#
+# Device specifications
+#
+[devices]
+# Pass-through devices.
+# Name Base-Ipa Base-Pa Length Alloc-Irq.
+passthrough_devices = [
+    # ["/soc/serial@10000000", 0x1000_0000, 0x1000_0000, 0x1000, 33],
+]
+
+# Passthrough addresses.
+# Base-GPA  Length.
+passthrough_addresses = [
+    [0x1000_0000, 0x1000],     # uart
+    [0x1000_1000, 0x8000],     # virtio-mmio
+]
+
+# Devices that are not desired to be passed through to the guest
+excluded_devices = [
+]
+
+# Emu_devices.
+# Name Base-Ipa Ipa_len Alloc-Irq Emu-Type EmuConfig.
+emu_devices = [
+    ["plic", 0x0c00_0000, 0x60_0000, 0, 0x30, [2]],     # [context_num]
+]
+
+interrupt_mode = "passthrough"