| | |
| | |
| | |
| | |
| | |
| | |
| | |
| | |
| | |
| | |
| | |
| | |
| | |
| |
|
| | #include "clip_riscv.h" |
| |
|
| | #if __riscv_vector |
| | #include <riscv_vector.h> |
| | #include "rvv_mathfun.h" |
| | #include "rvv_mathfun_fp16s.h" |
| | #endif |
| |
|
| | namespace ncnn { |
| |
|
| | Clip_riscv::Clip_riscv() |
| | { |
| | #if __riscv_vector |
| | support_packing = true; |
| | #if __riscv_zfh |
| | support_fp16_storage = true; |
| | #endif |
| | #endif |
| | } |
| |
|
| | int Clip_riscv::forward_inplace(Mat& bottom_top_blob, const Option& opt) const |
| | { |
| | #if __riscv_vector && __riscv_zfh |
| | int elembits = bottom_top_blob.elembits(); |
| |
|
| | if (opt.use_fp16_storage && elembits == 16) |
| | { |
| | if (opt.use_fp16_arithmetic) |
| | return forward_inplace_fp16sa(bottom_top_blob, opt); |
| | else |
| | return forward_inplace_fp16s(bottom_top_blob, opt); |
| | } |
| | #endif |
| |
|
| | int w = bottom_top_blob.w; |
| | int h = bottom_top_blob.h; |
| | int d = bottom_top_blob.d; |
| | int channels = bottom_top_blob.c; |
| | int elempack = bottom_top_blob.elempack; |
| | int size = w * h * d * elempack; |
| |
|
| | #pragma omp parallel for num_threads(opt.num_threads) |
| | for (int q = 0; q < channels; q++) |
| | { |
| | float* ptr = bottom_top_blob.channel(q); |
| |
|
| | #if __riscv_vector |
| | int n = size; |
| | while (n > 0) |
| | { |
| | size_t vl = vsetvl_e32m8(n); |
| |
|
| | vfloat32m8_t _p = vle32_v_f32m8(ptr, vl); |
| | _p = vfmax_vf_f32m8(_p, min, vl); |
| | _p = vfmin_vf_f32m8(_p, max, vl); |
| | vse32_v_f32m8(ptr, _p, vl); |
| |
|
| | ptr += vl; |
| | n -= vl; |
| | } |
| | #else |
| | for (int i = 0; i < size; i++) |
| | { |
| | if (*ptr < min) |
| | *ptr = min; |
| |
|
| | if (*ptr > max) |
| | *ptr = max; |
| |
|
| | ptr++; |
| | } |
| | #endif |
| | } |
| |
|
| | return 0; |
| | } |
| |
|
| | #if __riscv_vector && __riscv_zfh |
| | int Clip_riscv::forward_inplace_fp16s(Mat& bottom_top_blob, const Option& opt) const |
| | { |
| | int w = bottom_top_blob.w; |
| | int h = bottom_top_blob.h; |
| | int d = bottom_top_blob.d; |
| | int channels = bottom_top_blob.c; |
| | int elempack = bottom_top_blob.elempack; |
| | int size = w * h * d * elempack; |
| |
|
| | #pragma omp parallel for num_threads(opt.num_threads) |
| | for (int q = 0; q < channels; q++) |
| | { |
| | __fp16* ptr = bottom_top_blob.channel(q); |
| |
|
| | int n = size; |
| | while (n > 0) |
| | { |
| | size_t vl = vsetvl_e16m4(n); |
| |
|
| | vfloat32m8_t _p = vfwcvt_f_f_v_f32m8(vle16_v_f16m4(ptr, vl), vl); |
| | _p = vfmax_vf_f32m8(_p, min, vl); |
| | _p = vfmin_vf_f32m8(_p, max, vl); |
| | vse16_v_f16m4(ptr, vfncvt_f_f_w_f16m4(_p, vl), vl); |
| |
|
| | ptr += vl; |
| | n -= vl; |
| | } |
| | } |
| |
|
| | return 0; |
| | } |
| |
|
| | int Clip_riscv::forward_inplace_fp16sa(Mat& bottom_top_blob, const Option& opt) const |
| | { |
| | int w = bottom_top_blob.w; |
| | int h = bottom_top_blob.h; |
| | int d = bottom_top_blob.d; |
| | int channels = bottom_top_blob.c; |
| | int elempack = bottom_top_blob.elempack; |
| | int size = w * h * d * elempack; |
| |
|
| | #pragma omp parallel for num_threads(opt.num_threads) |
| | for (int q = 0; q < channels; q++) |
| | { |
| | __fp16* ptr = bottom_top_blob.channel(q); |
| |
|
| | int n = size; |
| | while (n > 0) |
| | { |
| | size_t vl = vsetvl_e16m8(n); |
| |
|
| | vfloat16m8_t _p = vle16_v_f16m8(ptr, vl); |
| | _p = vfmax_vf_f16m8(_p, min, vl); |
| | _p = vfmin_vf_f16m8(_p, max, vl); |
| | vse16_v_f16m8(ptr, _p, vl); |
| |
|
| | ptr += vl; |
| | n -= vl; |
| | } |
| | } |
| |
|
| | return 0; |
| | } |
| | #endif |
| |
|
| | } |
| |
|