hipBLAS

rocBLAS（AMD）と cuBLAS（NVIDIA）の統一インターフェースを提供する BLAS marshalling ライブラリです。アプリケーション側のコード変更なしに backend を切り替えられます。ggml-hip は vendors/hip.h で CUDA API を hipBLAS 等価物にリマップし、BLAS fallback 経路の入口として機能します。

A BLAS marshalling library providing a unified interface across rocBLAS (AMD) and cuBLAS (NVIDIA). Allows backend switching without changing application code. ggml-hip remaps CUDA APIs to hipBLAS equivalents via vendors/hip.h, making hipBLAS the gateway for the BLAS fallback path.

libhipblas.so.2.3.60303 RX9070XT: 依存チェーン確認済み RX9070XT: Dependency chain confirmed

ROCm スタックにおける位置づけPosition in the ROCm Stack

hipBLAS は rocBLAS の上位 abstraction 層として機能します。GPU アーキテクチャ固有の最適化は rocBLAS / Tensile が担い、hipBLAS はその API ラッパーです。gfx1201 固有のコードは hipBLAS には含まれず、バックエンドの rocBLAS から継承されます。

hipBLAS functions as an abstraction layer above rocBLAS. GPU architecture-specific optimizations are handled by rocBLAS/Tensile; hipBLAS is their API wrapper. gfx1201-specific code is not in hipBLAS itself — it is inherited from the rocBLAS backend.

ggml-hip (BLAS fallback 経路BLAS fallback path) ↓ ggml_cuda_op_mul_mat_cublas() ↓ hipBLAS （vendors/hip.h で cublasGemmEx → hipblasGemmEx にリマップ）(cublasGemmEx → hipblasGemmEx remapped via vendors/hip.h) ↓ rocBLAS ↓ Tensile kernel (Cijk_* / gfx1201)

観測済み事実（RX9070XT）Observed Facts (RX9070XT)

ldd /usr/local/lib/ollama/rocm/libggml-hip.so で libhipblas.so.2.3.60303 が直接依存として確認されました（Phase C）。
ggml の vendors/hip.h ソースで cublasCreate・cublasGemmEx・cublasSgemm 等が hipBLAS 等価物にリマップされていることを確認しました（Phase B）。
同 header に rocblas/rocblas.h の include と rocblas_initialize() 呼び出しも含まれており、hipBLAS を通じた rocBLAS の直接 initialize もここで行われます。
RX9070XT live case での ROCBLAS_LAYER=9 ログには rocblas_create_handle のみが記録され、これが hipBLAS 経由の handle 初期化に対応する可能性があります。

ldd /usr/local/lib/ollama/rocm/libggml-hip.so confirmed libhipblas.so.2.3.60303 as a direct dependency (Phase C).
Source-confirmed in ggml's vendors/hip.h that cublasCreate, cublasGemmEx, cublasSgemm, etc. are remapped to hipBLAS equivalents (Phase B).
The same header also includes rocblas/rocblas.h and calls rocblas_initialize() directly, so rocBLAS initialization also occurs here via hipBLAS.
The ROCBLAS_LAYER=9 log from the RX9070XT live case only recorded rocblas_create_handle — which may correspond to the handle initialization via hipBLAS.

未確定事項Open Questions

RX9070XT の live short case で hipBLAS/rocBLAS BLAS fallback が実際に GEMM dispatch を行ったかは未確定です。
hipBLAS 固有の挙動（rocBLAS を介さない固有パス）が LLM 推論結果へ与える影響は未確定です。

Whether hipBLAS/rocBLAS BLAS fallback actually dispatched GEMM in the RX9070XT live short case remains unresolved.
Any hipBLAS-specific behavior (paths not going through rocBLAS) and its impact on LLM inference results are undetermined.

掲載情報は観測記録に基づきます。未確定事項は確定次第更新します。 Content is grounded in observation logs. Open questions are updated as findings solidify.