feat(rknpu): make rknpu to hole crates

Author: Dirinkbottle

.cargo/config.toml

@@ -0,0 +1,3 @@
+[target.'cfg(all(target_os = "none"))']
+# runner = "ostool cargo-test"
+runner = "cargo osrun"

.github/workflows/ci.yml

@@ -0,0 +1,53 @@
+name: Test CI
+
+on: [push, pull_request]
+
+jobs:
+  clippy:
+    runs-on: ubuntu-22.04
+    strategy:
+      fail-fast: false
+    env:
+      RUSTUP_TOOLCHAIN: nightly
+    steps:
+    - uses: actions/checkout@v4
+    - uses: dtolnay/rust-toolchain@stable
+      with:
+        toolchain: nightly
+        components: rust-src, clippy, rustfmt
+        targets: aarch64-unknown-none-softfloat
+    - uses: Swatinem/rust-cache@v2
+      with:
+        shared-key: cargo-bin-cache
+        cache-targets: false
+    - name: Check rust version
+      run: rustc --version --verbose
+    - name: Check code format
+      run: cargo fmt --all -- --check
+    - name: Clippy for the default target
+      run: cargo clippy
+
+  Test:
+    runs-on: ubuntu-22.04
+    strategy:
+      fail-fast: false
+      matrix:
+        rust-toolchain: [nightly]
+    env:
+      RUSTUP_TOOLCHAIN: ${{ matrix.rust-toolchain }}
+    steps:
+    - uses: actions/checkout@v4
+    - uses: dtolnay/rust-toolchain@stable
+      with:
+        toolchain: ${{ matrix.rust-toolchain }}
+        components: rust-src, llvm-tools
+        targets: aarch64-unknown-none-softfloat
+    - uses: Swatinem/rust-cache@v2
+      with:
+        shared-key: cargo-bin-cache
+        cache-targets: false
+    - run: sudo apt update && sudo apt install -y libudev-dev
+    - run: cargo install cargo-binutils
+    - run: cargo install ostool@0.7.24 
+    - name: Build
+      run: cargo build

.gitignore

@@ -0,0 +1,4 @@
+/target
+Cargo.lock
+.bare-test.toml
+.spec-workflow

.vscode/launch.json

@@ -0,0 +1,18 @@
+{
+    // 使用 IntelliSense 了解相关属性。 
+    // 悬停以查看现有属性的描述。
+    // 欲了解更多信息，请访问: https://go.microsoft.com/fwlink/?linkid=830387
+    "version": "0.2.0",
+    "configurations": [
+        {
+            "type": "cppdbg",
+            "name": "Debug Test",
+            "request": "launch",
+            "miDebuggerServerAddress": "localhost:1234",
+            "program": "${workspaceFolder}/target/kernel.elf",
+            "miDebuggerPath": "gdb-multiarch",
+            "cwd": "${workspaceRoot}",
+            "preLaunchTask": "debug test"
+        },
+    ]
+}

.vscode/settings.json

@@ -0,0 +1,4 @@
+{
+    "rust-analyzer.cargo.allTargets": false,
+    "rust-analyzer.cargo.target": "aarch64-unknown-none-softfloat",
+}

.vscode/tasks.json

@@ -0,0 +1,35 @@
+{
+	"version": "2.0.0",
+	"tasks": [
+		{
+			"type": "shell",
+			"label": "debug test",
+			"command": "cargo",
+			"args": [
+				"test",
+				"--test",
+				"test",
+				"--",
+				"--show-output",
+				"--no-run",
+			],
+			"options": {
+				"cwd": "${fileDirname}"
+			},
+			"problemMatcher": {
+				"base": "$rustc",
+				"background": {
+					"activeOnStart": true,
+					"beginsPattern": "^.*",
+					"endsPattern": "^.*Running tests"
+				}
+			},
+			"group": {
+				"kind": "test",
+				"isDefault": true
+			},
+			"detail": "断点调试 test 测试用例",
+			"isBackground": true,
+		}
+	]
+}

Cargo.toml

@@ -0,0 +1,21 @@
+[package]
+edition = "2024"
+name = "rknpu"
+version = "0.1.0"
+
+[features]
+default = []
+starryos = []
+
+[dependencies]
+aarch64-cpu-ext = "0.1"
+dma-api = {version = "0.5.2", features = ["alloc"]}
+log = "0.4"
+mbarrier = "0.1"
+num-align = "0.1"
+rdif-base = {version = "0.7"}
+spin = "0.10"
+thiserror = {version = "2.0", default-features = false}
+bitflags = "2"
+rknpu-regs = {path = "../rknpu-regs"}
+

bare-test.toml

@@ -0,0 +1,5 @@
+[qemu]
+machine = "virt"
+cpu = "cortex-a53"
+graphic = false
+args = ""

build.rs

@@ -0,0 +1 @@
+fn main() {}