opencv
diff --git a/‎3rdparty/hal_rvv/hal_rvv.hpp
Copy file name to clipboard
+1Lines changed: 1 addition & 0 deletions b/‎3rdparty/hal_rvv/hal_rvv.hpp
Copy file name to clipboard
+1Lines changed: 1 addition & 0 deletions
diff --git a/‎3rdparty/hal_rvv/hal_rvv_1p0/common.hpp
Copy file name to clipboard
+22Lines changed: 22 additions & 0 deletions b/‎3rdparty/hal_rvv/hal_rvv_1p0/common.hpp
Copy file name to clipboard
+22Lines changed: 22 additions & 0 deletions
diff --git a/‎3rdparty/hal_rvv/hal_rvv_1p0/norm.hpp
Copy file name to clipboard
+3-2Lines changed: 3 additions & 2 deletions b/‎3rdparty/hal_rvv/hal_rvv_1p0/norm.hpp
Copy file name to clipboard
+3-2Lines changed: 3 additions & 2 deletions
@@ -5,6 +5,7 @@
 #ifndef OPENCV_HAL_RVV_HPP_INCLUDED
 #define OPENCV_HAL_RVV_HPP_INCLUDED
 
+#include "opencv2/core/base.hpp"
 #include "opencv2/core/hal/interface.h"
 #include "opencv2/imgproc/hal/interface.h"
 
 
@@ -1,6 +1,9 @@
 // This file is part of OpenCV project.
 // It is subject to the license terms in the LICENSE file found in the top-level directory
 // of this distribution and at https://opencv.org/license.html.
+//
+// Copyright (C) 2025, SpaceMIT Inc., all rights reserved.
+// Third party copyrights are property of their respective owners.
 
 #ifndef OPENCV_HAL_RVV_COMMON_HPP_INCLUDED
 #define OPENCV_HAL_RVV_COMMON_HPP_INCLUDED
@@ -9,6 +12,8 @@
 
 namespace cv { namespace cv_hal_rvv { namespace custom_intrin {
 
+#define CV_HAL_RVV_NOOP(a) (a)
+
 #define CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABS(_Tpvs, _Tpvd, shift, suffix) \
     inline _Tpvd __riscv_vabs(const _Tpvs& v, const int vl) { \
         _Tpvs mask = __riscv_vsra(v, shift, vl); \
@@ -25,6 +30,23 @@ CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABS(vint16m8_t, vuint16m8_t, 15, u16m8)
 CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABS(vint32m4_t, vuint32m4_t, 31, u32m4)
 CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABS(vint32m8_t, vuint32m8_t, 31, u32m8)
 
+#define CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(_Tpvs, _Tpvd, cast, sub, max, min) \
+    inline _Tpvd __riscv_vabd(const _Tpvs& v1, const _Tpvs& v2, const int vl) { \
+        return cast(__riscv_##sub(__riscv_##max(v1, v2, vl), __riscv_##min(v1, v2, vl), vl)); \
+    }
+
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vuint8m4_t, vuint8m4_t, CV_HAL_RVV_NOOP, vsub, vmaxu, vminu)
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vuint8m8_t, vuint8m8_t, CV_HAL_RVV_NOOP, vsub, vmaxu, vminu)
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vuint16m2_t, vuint16m2_t, CV_HAL_RVV_NOOP, vsub, vmaxu, vminu)
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vuint16m8_t, vuint16m8_t, CV_HAL_RVV_NOOP, vsub, vmaxu, vminu)
+
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vint8m4_t, vuint8m4_t, __riscv_vreinterpret_u8m4, vsub, vmax, vmin)
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vint8m8_t, vuint8m8_t, __riscv_vreinterpret_u8m8, vsub, vmax, vmin)
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vint16m2_t, vuint16m2_t, __riscv_vreinterpret_u16m2, vsub, vmax, vmin)
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vint16m8_t, vuint16m8_t, __riscv_vreinterpret_u16m8, vsub, vmax, vmin)
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vint32m4_t, vuint32m4_t, __riscv_vreinterpret_u32m4, vsub, vmax, vmin)
+CV_HAL_RVV_COMMON_CUSTOM_INTRIN_ABSDIFF(vint32m8_t, vuint32m8_t, __riscv_vreinterpret_u32m8, vsub, vmax, vmin)
+
 }}} // cv::cv_hal_rvv::custom_intrin
 
 #endif
@@ -166,7 +166,7 @@ struct NormL1_RVV<uchar, int> {
         for (int i = 0; i < n; i += vl) {
             vl = __riscv_vsetvl_e8m8(n - i);
             auto v = __riscv_vle8_v_u8m8(src + i, vl);
-            s = __riscv_vwredsumu(__riscv_vwredsumu_tu(zero, v, zero, vl), s, vl);
+            s = __riscv_vwredsumu(__riscv_vwredsumu_tu(zero, v, zero, vl), s, __riscv_vsetvlmax_e16m1());
         }
         return __riscv_vmv_x(s);
     }
@@ -181,7 +181,7 @@ struct NormL1_RVV<schar, int> {
         for (int i = 0; i < n; i += vl) {
             vl = __riscv_vsetvl_e8m8(n - i);
             auto v = custom_intrin::__riscv_vabs(__riscv_vle8_v_i8m8(src + i, vl), vl);
-            s = __riscv_vwredsumu(__riscv_vwredsumu_tu(zero, v, zero, vl), s, vl);
+            s = __riscv_vwredsumu(__riscv_vwredsumu_tu(zero, v, zero, vl), s, __riscv_vsetvlmax_e16m1());
         }
         return __riscv_vmv_x(s);
     }
@@ -1008,6 +1008,7 @@ inline int norm(const uchar* src, size_t src_step, const uchar* mask, size_t mas
         sizeof(int),     sizeof(float),
         sizeof(int64_t), 0,
     };
+    CV_Assert(elem_size_tab[depth]);
 
     bool src_continuous = (src_step == width * elem_size_tab[depth] * cn || (src_step != width * elem_size_tab[depth] * cn && height == 1));
     bool mask_continuous = (mask_step == static_cast<size_t>(width));
Original file line number	Diff line number	Diff line change
`@@ -166,7 +166,7 @@ struct NormL1_RVV<uchar, int> {`
`166`	`166`	`for (int i = 0; i < n; i += vl) {`
`167`	`167`	`vl = __riscv_vsetvl_e8m8(n - i);`
`168`	`168`	`auto v = __riscv_vle8_v_u8m8(src + i, vl);`
`169`		`- s = __riscv_vwredsumu(__riscv_vwredsumu_tu(zero, v, zero, vl), s, vl);`
	`169`	`+ s = __riscv_vwredsumu(__riscv_vwredsumu_tu(zero, v, zero, vl), s, __riscv_vsetvlmax_e16m1());`
`170`	`170`	`}`
`171`	`171`	`return __riscv_vmv_x(s);`
`172`	`172`	`}`
`@@ -181,7 +181,7 @@ struct NormL1_RVV<schar, int> {`
`181`	`181`	`for (int i = 0; i < n; i += vl) {`
`182`	`182`	`vl = __riscv_vsetvl_e8m8(n - i);`
`183`	`183`	`auto v = custom_intrin::__riscv_vabs(__riscv_vle8_v_i8m8(src + i, vl), vl);`
`184`		`- s = __riscv_vwredsumu(__riscv_vwredsumu_tu(zero, v, zero, vl), s, vl);`
	`184`	`+ s = __riscv_vwredsumu(__riscv_vwredsumu_tu(zero, v, zero, vl), s, __riscv_vsetvlmax_e16m1());`
`185`	`185`	`}`
`186`	`186`	`return __riscv_vmv_x(s);`
`187`	`187`	`}`
`@@ -1008,6 +1008,7 @@ inline int norm(const uchar* src, size_t src_step, const uchar* mask, size_t mas`
`1008`	`1008`	`sizeof(int), sizeof(float),`
`1009`	`1009`	`sizeof(int64_t), 0,`
`1010`	`1010`	`};`
	`1011`	`+ CV_Assert(elem_size_tab[depth]);`
`1011`	`1012`
`1012`	`1013`	`bool src_continuous = (src_step == width * elem_size_tab[depth] * cn \|\| (src_step != width * elem_size_tab[depth] * cn && height == 1));`
`1013`	`1014`	`bool mask_continuous = (mask_step == static_cast<size_t>(width));`