Skip to content

Add permutation intrinsics for zvfbfmin #408

New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

Sign up for GitHub

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Merged
merged 3 commits into from
Sep 5, 2025
Merged

Add permutation intrinsics for zvfbfmin #408

Show file tree
Hide file tree
Changes from all commits
Commits
Show all changes
3 commits
Select commit Hold shift + click to select a range
d67d2d6
Add permutation intrinsics for zvfbfmin
tclin914 Jun 27, 2025
1c4f9c6
[Auto-gen] Update bfloat16 documents under ../auto-generated. (make g…
tclin914 Jul 11, 2025
36723fb
[Auto-gen] Update bfloat16 tests under ../auto-generated. (make git-c…
tclin914 Jul 11, 2025
File filter

Filter by extension

Filter by extension
Conversations
Failed to load comments.
Loading
Jump to
Jump to file
Failed to load files.
Loading
Diff view
Diff view
32 changes: 32 additions & 0 deletions auto-generated/bfloat16/api-testing/vcompress.c
View file
Open in desktop
Original file line number Diff line number Diff line change
@@ -0,0 +1,32 @@
#include <riscv_vector.h>
#include <stdint.h>

vbfloat16mf4_t test_vcompress_vm_bf16mf4(vbfloat16mf4_t vs2, vbool64_t vs1,
size_t vl) {
return __riscv_vcompress_vm_bf16mf4(vs2, vs1, vl);
}

vbfloat16mf2_t test_vcompress_vm_bf16mf2(vbfloat16mf2_t vs2, vbool32_t vs1,
size_t vl) {
return __riscv_vcompress_vm_bf16mf2(vs2, vs1, vl);
}

vbfloat16m1_t test_vcompress_vm_bf16m1(vbfloat16m1_t vs2, vbool16_t vs1,
size_t vl) {
return __riscv_vcompress_vm_bf16m1(vs2, vs1, vl);
}

vbfloat16m2_t test_vcompress_vm_bf16m2(vbfloat16m2_t vs2, vbool8_t vs1,
size_t vl) {
return __riscv_vcompress_vm_bf16m2(vs2, vs1, vl);
}

vbfloat16m4_t test_vcompress_vm_bf16m4(vbfloat16m4_t vs2, vbool4_t vs1,
size_t vl) {
return __riscv_vcompress_vm_bf16m4(vs2, vs1, vl);
}

vbfloat16m8_t test_vcompress_vm_bf16m8(vbfloat16m8_t vs2, vbool2_t vs1,
size_t vl) {
return __riscv_vcompress_vm_bf16m8(vs2, vs1, vl);
}
122 changes: 122 additions & 0 deletions auto-generated/bfloat16/api-testing/vrgather.c
View file
Open in desktop
Original file line number Diff line number Diff line change
@@ -0,0 +1,122 @@
#include <riscv_vector.h>
#include <stdint.h>

vbfloat16mf4_t test_vrgather_vv_bf16mf4(vbfloat16mf4_t vs2, vuint16mf4_t vs1,
size_t vl) {
return __riscv_vrgather_vv_bf16mf4(vs2, vs1, vl);
}

vbfloat16mf4_t test_vrgather_vx_bf16mf4(vbfloat16mf4_t vs2, size_t vs1,
size_t vl) {
return __riscv_vrgather_vx_bf16mf4(vs2, vs1, vl);
}

vbfloat16mf2_t test_vrgather_vv_bf16mf2(vbfloat16mf2_t vs2, vuint16mf2_t vs1,
size_t vl) {
return __riscv_vrgather_vv_bf16mf2(vs2, vs1, vl);
}

vbfloat16mf2_t test_vrgather_vx_bf16mf2(vbfloat16mf2_t vs2, size_t vs1,
size_t vl) {
return __riscv_vrgather_vx_bf16mf2(vs2, vs1, vl);
}

vbfloat16m1_t test_vrgather_vv_bf16m1(vbfloat16m1_t vs2, vuint16m1_t vs1,
size_t vl) {
return __riscv_vrgather_vv_bf16m1(vs2, vs1, vl);
}

vbfloat16m1_t test_vrgather_vx_bf16m1(vbfloat16m1_t vs2, size_t vs1,
size_t vl) {
return __riscv_vrgather_vx_bf16m1(vs2, vs1, vl);
}

vbfloat16m2_t test_vrgather_vv_bf16m2(vbfloat16m2_t vs2, vuint16m2_t vs1,
size_t vl) {
return __riscv_vrgather_vv_bf16m2(vs2, vs1, vl);
}

vbfloat16m2_t test_vrgather_vx_bf16m2(vbfloat16m2_t vs2, size_t vs1,
size_t vl) {
return __riscv_vrgather_vx_bf16m2(vs2, vs1, vl);
}

vbfloat16m4_t test_vrgather_vv_bf16m4(vbfloat16m4_t vs2, vuint16m4_t vs1,
size_t vl) {
return __riscv_vrgather_vv_bf16m4(vs2, vs1, vl);
}

vbfloat16m4_t test_vrgather_vx_bf16m4(vbfloat16m4_t vs2, size_t vs1,
size_t vl) {
return __riscv_vrgather_vx_bf16m4(vs2, vs1, vl);
}

vbfloat16m8_t test_vrgather_vv_bf16m8(vbfloat16m8_t vs2, vuint16m8_t vs1,
size_t vl) {
return __riscv_vrgather_vv_bf16m8(vs2, vs1, vl);
}

vbfloat16m8_t test_vrgather_vx_bf16m8(vbfloat16m8_t vs2, size_t vs1,
size_t vl) {
return __riscv_vrgather_vx_bf16m8(vs2, vs1, vl);
}

vbfloat16mf4_t test_vrgather_vv_bf16mf4_m(vbool64_t vm, vbfloat16mf4_t vs2,
vuint16mf4_t vs1, size_t vl) {
return __riscv_vrgather_vv_bf16mf4_m(vm, vs2, vs1, vl);
}

vbfloat16mf4_t test_vrgather_vx_bf16mf4_m(vbool64_t vm, vbfloat16mf4_t vs2,
size_t vs1, size_t vl) {
return __riscv_vrgather_vx_bf16mf4_m(vm, vs2, vs1, vl);
}

vbfloat16mf2_t test_vrgather_vv_bf16mf2_m(vbool32_t vm, vbfloat16mf2_t vs2,
vuint16mf2_t vs1, size_t vl) {
return __riscv_vrgather_vv_bf16mf2_m(vm, vs2, vs1, vl);
}

vbfloat16mf2_t test_vrgather_vx_bf16mf2_m(vbool32_t vm, vbfloat16mf2_t vs2,
size_t vs1, size_t vl) {
return __riscv_vrgather_vx_bf16mf2_m(vm, vs2, vs1, vl);
}

vbfloat16m1_t test_vrgather_vv_bf16m1_m(vbool16_t vm, vbfloat16m1_t vs2,
vuint16m1_t vs1, size_t vl) {
return __riscv_vrgather_vv_bf16m1_m(vm, vs2, vs1, vl);
}

vbfloat16m1_t test_vrgather_vx_bf16m1_m(vbool16_t vm, vbfloat16m1_t vs2,
size_t vs1, size_t vl) {
return __riscv_vrgather_vx_bf16m1_m(vm, vs2, vs1, vl);
}

vbfloat16m2_t test_vrgather_vv_bf16m2_m(vbool8_t vm, vbfloat16m2_t vs2,
vuint16m2_t vs1, size_t vl) {
return __riscv_vrgather_vv_bf16m2_m(vm, vs2, vs1, vl);
}

vbfloat16m2_t test_vrgather_vx_bf16m2_m(vbool8_t vm, vbfloat16m2_t vs2,
size_t vs1, size_t vl) {
return __riscv_vrgather_vx_bf16m2_m(vm, vs2, vs1, vl);
}

vbfloat16m4_t test_vrgather_vv_bf16m4_m(vbool4_t vm, vbfloat16m4_t vs2,
vuint16m4_t vs1, size_t vl) {
return __riscv_vrgather_vv_bf16m4_m(vm, vs2, vs1, vl);
}

vbfloat16m4_t test_vrgather_vx_bf16m4_m(vbool4_t vm, vbfloat16m4_t vs2,
size_t vs1, size_t vl) {
return __riscv_vrgather_vx_bf16m4_m(vm, vs2, vs1, vl);
}

vbfloat16m8_t test_vrgather_vv_bf16m8_m(vbool2_t vm, vbfloat16m8_t vs2,
vuint16m8_t vs1, size_t vl) {
return __riscv_vrgather_vv_bf16m8_m(vm, vs2, vs1, vl);
}

vbfloat16m8_t test_vrgather_vx_bf16m8_m(vbool2_t vm, vbfloat16m8_t vs2,
size_t vs1, size_t vl) {
return __riscv_vrgather_vx_bf16m8_m(vm, vs2, vs1, vl);
}
62 changes: 62 additions & 0 deletions auto-generated/bfloat16/api-testing/vrgatherei16.c
View file
Open in desktop
Original file line number Diff line number Diff line change
@@ -0,0 +1,62 @@
#include <riscv_vector.h>
#include <stdint.h>

vbfloat16mf4_t test_vrgatherei16_vv_bf16mf4(vbfloat16mf4_t vs2,
vuint16mf4_t vs1, size_t vl) {
return __riscv_vrgatherei16_vv_bf16mf4(vs2, vs1, vl);
}

vbfloat16mf2_t test_vrgatherei16_vv_bf16mf2(vbfloat16mf2_t vs2,
vuint16mf2_t vs1, size_t vl) {
return __riscv_vrgatherei16_vv_bf16mf2(vs2, vs1, vl);
}

vbfloat16m1_t test_vrgatherei16_vv_bf16m1(vbfloat16m1_t vs2, vuint16m1_t vs1,
size_t vl) {
return __riscv_vrgatherei16_vv_bf16m1(vs2, vs1, vl);
}

vbfloat16m2_t test_vrgatherei16_vv_bf16m2(vbfloat16m2_t vs2, vuint16m2_t vs1,
size_t vl) {
return __riscv_vrgatherei16_vv_bf16m2(vs2, vs1, vl);
}

vbfloat16m4_t test_vrgatherei16_vv_bf16m4(vbfloat16m4_t vs2, vuint16m4_t vs1,
size_t vl) {
return __riscv_vrgatherei16_vv_bf16m4(vs2, vs1, vl);
}

vbfloat16m8_t test_vrgatherei16_vv_bf16m8(vbfloat16m8_t vs2, vuint16m8_t vs1,
size_t vl) {
return __riscv_vrgatherei16_vv_bf16m8(vs2, vs1, vl);
}

vbfloat16mf4_t test_vrgatherei16_vv_bf16mf4_m(vbool64_t vm, vbfloat16mf4_t vs2,
vuint16mf4_t vs1, size_t vl) {
return __riscv_vrgatherei16_vv_bf16mf4_m(vm, vs2, vs1, vl);
}

vbfloat16mf2_t test_vrgatherei16_vv_bf16mf2_m(vbool32_t vm, vbfloat16mf2_t vs2,
vuint16mf2_t vs1, size_t vl) {
return __riscv_vrgatherei16_vv_bf16mf2_m(vm, vs2, vs1, vl);
}

vbfloat16m1_t test_vrgatherei16_vv_bf16m1_m(vbool16_t vm, vbfloat16m1_t vs2,
vuint16m1_t vs1, size_t vl) {
return __riscv_vrgatherei16_vv_bf16m1_m(vm, vs2, vs1, vl);
}

vbfloat16m2_t test_vrgatherei16_vv_bf16m2_m(vbool8_t vm, vbfloat16m2_t vs2,
vuint16m2_t vs1, size_t vl) {
return __riscv_vrgatherei16_vv_bf16m2_m(vm, vs2, vs1, vl);
}

vbfloat16m4_t test_vrgatherei16_vv_bf16m4_m(vbool4_t vm, vbfloat16m4_t vs2,
vuint16m4_t vs1, size_t vl) {
return __riscv_vrgatherei16_vv_bf16m4_m(vm, vs2, vs1, vl);
}

vbfloat16m8_t test_vrgatherei16_vv_bf16m8_m(vbool2_t vm, vbfloat16m8_t vs2,
vuint16m8_t vs1, size_t vl) {
return __riscv_vrgatherei16_vv_bf16m8_m(vm, vs2, vs1, vl);
}
62 changes: 62 additions & 0 deletions auto-generated/bfloat16/api-testing/vslidedown.c
View file
Open in desktop
Original file line number Diff line number Diff line change
@@ -0,0 +1,62 @@
#include <riscv_vector.h>
#include <stdint.h>

vbfloat16mf4_t test_vslidedown_vx_bf16mf4(vbfloat16mf4_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslidedown_vx_bf16mf4(vs2, rs1, vl);
}

vbfloat16mf2_t test_vslidedown_vx_bf16mf2(vbfloat16mf2_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslidedown_vx_bf16mf2(vs2, rs1, vl);
}

vbfloat16m1_t test_vslidedown_vx_bf16m1(vbfloat16m1_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslidedown_vx_bf16m1(vs2, rs1, vl);
}

vbfloat16m2_t test_vslidedown_vx_bf16m2(vbfloat16m2_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslidedown_vx_bf16m2(vs2, rs1, vl);
}

vbfloat16m4_t test_vslidedown_vx_bf16m4(vbfloat16m4_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslidedown_vx_bf16m4(vs2, rs1, vl);
}

vbfloat16m8_t test_vslidedown_vx_bf16m8(vbfloat16m8_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslidedown_vx_bf16m8(vs2, rs1, vl);
}

vbfloat16mf4_t test_vslidedown_vx_bf16mf4_m(vbool64_t vm, vbfloat16mf4_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslidedown_vx_bf16mf4_m(vm, vs2, rs1, vl);
}

vbfloat16mf2_t test_vslidedown_vx_bf16mf2_m(vbool32_t vm, vbfloat16mf2_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslidedown_vx_bf16mf2_m(vm, vs2, rs1, vl);
}

vbfloat16m1_t test_vslidedown_vx_bf16m1_m(vbool16_t vm, vbfloat16m1_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslidedown_vx_bf16m1_m(vm, vs2, rs1, vl);
}

vbfloat16m2_t test_vslidedown_vx_bf16m2_m(vbool8_t vm, vbfloat16m2_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslidedown_vx_bf16m2_m(vm, vs2, rs1, vl);
}

vbfloat16m4_t test_vslidedown_vx_bf16m4_m(vbool4_t vm, vbfloat16m4_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslidedown_vx_bf16m4_m(vm, vs2, rs1, vl);
}

vbfloat16m8_t test_vslidedown_vx_bf16m8_m(vbool2_t vm, vbfloat16m8_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslidedown_vx_bf16m8_m(vm, vs2, rs1, vl);
}
68 changes: 68 additions & 0 deletions auto-generated/bfloat16/api-testing/vslideup.c
View file
Open in desktop
Original file line number Diff line number Diff line change
@@ -0,0 +1,68 @@
#include <riscv_vector.h>
#include <stdint.h>

vbfloat16mf4_t test_vslideup_vx_bf16mf4(vbfloat16mf4_t vd, vbfloat16mf4_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslideup_vx_bf16mf4(vd, vs2, rs1, vl);
}

vbfloat16mf2_t test_vslideup_vx_bf16mf2(vbfloat16mf2_t vd, vbfloat16mf2_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslideup_vx_bf16mf2(vd, vs2, rs1, vl);
}

vbfloat16m1_t test_vslideup_vx_bf16m1(vbfloat16m1_t vd, vbfloat16m1_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslideup_vx_bf16m1(vd, vs2, rs1, vl);
}

vbfloat16m2_t test_vslideup_vx_bf16m2(vbfloat16m2_t vd, vbfloat16m2_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslideup_vx_bf16m2(vd, vs2, rs1, vl);
}

vbfloat16m4_t test_vslideup_vx_bf16m4(vbfloat16m4_t vd, vbfloat16m4_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslideup_vx_bf16m4(vd, vs2, rs1, vl);
}

vbfloat16m8_t test_vslideup_vx_bf16m8(vbfloat16m8_t vd, vbfloat16m8_t vs2,
size_t rs1, size_t vl) {
return __riscv_vslideup_vx_bf16m8(vd, vs2, rs1, vl);
}

vbfloat16mf4_t test_vslideup_vx_bf16mf4_m(vbool64_t vm, vbfloat16mf4_t vd,
vbfloat16mf4_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslideup_vx_bf16mf4_m(vm, vd, vs2, rs1, vl);
}

vbfloat16mf2_t test_vslideup_vx_bf16mf2_m(vbool32_t vm, vbfloat16mf2_t vd,
vbfloat16mf2_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslideup_vx_bf16mf2_m(vm, vd, vs2, rs1, vl);
}

vbfloat16m1_t test_vslideup_vx_bf16m1_m(vbool16_t vm, vbfloat16m1_t vd,
vbfloat16m1_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslideup_vx_bf16m1_m(vm, vd, vs2, rs1, vl);
}

vbfloat16m2_t test_vslideup_vx_bf16m2_m(vbool8_t vm, vbfloat16m2_t vd,
vbfloat16m2_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslideup_vx_bf16m2_m(vm, vd, vs2, rs1, vl);
}

vbfloat16m4_t test_vslideup_vx_bf16m4_m(vbool4_t vm, vbfloat16m4_t vd,
vbfloat16m4_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslideup_vx_bf16m4_m(vm, vd, vs2, rs1, vl);
}

vbfloat16m8_t test_vslideup_vx_bf16m8_m(vbool2_t vm, vbfloat16m8_t vd,
vbfloat16m8_t vs2, size_t rs1,
size_t vl) {
return __riscv_vslideup_vx_bf16m8_m(vm, vd, vs2, rs1, vl);
}
Loading