Home
last modified time | relevance | path

Searched refs:smem (Results 1 – 25 of 54) sorted by relevance

123

/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/cuda/detail/
H A Dreduce.hpp74 … static __device__ void loadToSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadToSmem()
76 thrust::get<I>(smem)[tid] = thrust::get<I>(val); in loadToSmem() local
78 For<I + 1, N>::loadToSmem(smem, val, tid); in loadToSmem()
81 …static __device__ void loadFromSmem(const PointerTuple& smem, const ValTuple& val, unsigned int ti… in loadFromSmem()
83 thrust::get<I>(val) = thrust::get<I>(smem)[tid]; in loadFromSmem()
85 For<I + 1, N>::loadFromSmem(smem, val, tid); in loadFromSmem()
89 …static __device__ void merge(const PointerTuple& smem, const ValTuple& val, unsigned int tid, unsi… in merge()
91 …pename thrust::tuple_element<I, PointerTuple>::type>::type reg = thrust::get<I>(smem)[tid + delta]; in merge()
92 … thrust::get<I>(smem)[tid] = thrust::get<I>(val) = thrust::get<I>(op)(thrust::get<I>(val), reg); in merge() local
94 For<I + 1, N>::merge(smem, val, tid, delta, op); in merge()
[all …]
H A Dreduce_key_val.hpp74 …static __device__ void loadToSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned i… in loadToSmem()
76 thrust::get<I>(smem)[tid] = thrust::get<I>(data); in loadToSmem() local
78 For<I + 1, N>::loadToSmem(smem, data, tid); in loadToSmem()
81 …static __device__ void loadFromSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned… in loadFromSmem()
83 thrust::get<I>(data) = thrust::get<I>(smem)[tid]; in loadFromSmem()
85 For<I + 1, N>::loadFromSmem(smem, data, tid); in loadFromSmem()
171 __device__ __forceinline__ void loadToSmem(volatile T* smem, T& data, unsigned int tid) in loadToSmem() argument
173 smem[tid] = data; in loadToSmem()
176 __device__ __forceinline__ void loadFromSmem(volatile T* smem, T& data, unsigned int tid) in loadFromSmem() argument
178 data = smem[tid]; in loadFromSmem()
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/cuda/detail/
H A Dreduce.hpp74 … static __device__ void loadToSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadToSmem()
76 thrust::get<I>(smem)[tid] = thrust::get<I>(val); in loadToSmem() local
78 For<I + 1, N>::loadToSmem(smem, val, tid); in loadToSmem()
81 …static __device__ void loadFromSmem(const PointerTuple& smem, const ValTuple& val, unsigned int ti… in loadFromSmem()
83 thrust::get<I>(val) = thrust::get<I>(smem)[tid]; in loadFromSmem()
85 For<I + 1, N>::loadFromSmem(smem, val, tid); in loadFromSmem()
89 …static __device__ void merge(const PointerTuple& smem, const ValTuple& val, unsigned int tid, unsi… in merge()
91 …pename thrust::tuple_element<I, PointerTuple>::type>::type reg = thrust::get<I>(smem)[tid + delta]; in merge()
92 … thrust::get<I>(smem)[tid] = thrust::get<I>(val) = thrust::get<I>(op)(thrust::get<I>(val), reg); in merge() local
94 For<I + 1, N>::merge(smem, val, tid, delta, op); in merge()
[all …]
H A Dreduce_key_val.hpp74 …static __device__ void loadToSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned i… in loadToSmem()
76 thrust::get<I>(smem)[tid] = thrust::get<I>(data); in loadToSmem() local
78 For<I + 1, N>::loadToSmem(smem, data, tid); in loadToSmem()
81 …static __device__ void loadFromSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned… in loadFromSmem()
83 thrust::get<I>(data) = thrust::get<I>(smem)[tid]; in loadFromSmem()
85 For<I + 1, N>::loadFromSmem(smem, data, tid); in loadFromSmem()
171 __device__ __forceinline__ void loadToSmem(volatile T* smem, T& data, unsigned int tid) in loadToSmem() argument
173 smem[tid] = data; in loadToSmem()
176 __device__ __forceinline__ void loadFromSmem(volatile T* smem, T& data, unsigned int tid) in loadFromSmem() argument
178 data = smem[tid]; in loadFromSmem()
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/cuda/detail/
H A Dreduce.hpp74 … static __device__ void loadToSmem(const PointerTuple& smem, const ValTuple& val, unsigned int tid) in loadToSmem()
76 thrust::get<I>(smem)[tid] = thrust::get<I>(val); in loadToSmem() local
78 For<I + 1, N>::loadToSmem(smem, val, tid); in loadToSmem()
81 …static __device__ void loadFromSmem(const PointerTuple& smem, const ValTuple& val, unsigned int ti… in loadFromSmem()
83 thrust::get<I>(val) = thrust::get<I>(smem)[tid]; in loadFromSmem()
85 For<I + 1, N>::loadFromSmem(smem, val, tid); in loadFromSmem()
89 …static __device__ void merge(const PointerTuple& smem, const ValTuple& val, unsigned int tid, unsi… in merge()
91 …pename thrust::tuple_element<I, PointerTuple>::type>::type reg = thrust::get<I>(smem)[tid + delta]; in merge()
92 … thrust::get<I>(smem)[tid] = thrust::get<I>(val) = thrust::get<I>(op)(thrust::get<I>(val), reg); in merge() local
94 For<I + 1, N>::merge(smem, val, tid, delta, op); in merge()
[all …]
H A Dreduce_key_val.hpp74 …static __device__ void loadToSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned i… in loadToSmem()
76 thrust::get<I>(smem)[tid] = thrust::get<I>(data); in loadToSmem() local
78 For<I + 1, N>::loadToSmem(smem, data, tid); in loadToSmem()
81 …static __device__ void loadFromSmem(const PointerTuple& smem, const ReferenceTuple& data, unsigned… in loadFromSmem()
83 thrust::get<I>(data) = thrust::get<I>(smem)[tid]; in loadFromSmem()
85 For<I + 1, N>::loadFromSmem(smem, data, tid); in loadFromSmem()
171 __device__ __forceinline__ void loadToSmem(volatile T* smem, T& data, unsigned int tid) in loadToSmem() argument
173 smem[tid] = data; in loadToSmem()
176 __device__ __forceinline__ void loadFromSmem(volatile T* smem, T& data, unsigned int tid) in loadFromSmem() argument
178 data = smem[tid]; in loadFromSmem()
[all …]
/OK3568_Linux_fs/kernel/drivers/soc/qcom/
H A Dsmem.c348 static int qcom_smem_alloc_private(struct qcom_smem *smem, in qcom_smem_alloc_private() argument
373 dev_err(smem->dev, "Out of memory\n"); in qcom_smem_alloc_private()
393 dev_err(smem->dev, "Found invalid canary in hosts %hu:%hu partition\n", in qcom_smem_alloc_private()
399 static int qcom_smem_alloc_global(struct qcom_smem *smem, in qcom_smem_alloc_global() argument
406 header = smem->regions[0].virt_base; in qcom_smem_alloc_global()
481 static void *qcom_smem_get_global(struct qcom_smem *smem, in qcom_smem_get_global() argument
491 header = smem->regions[0].virt_base; in qcom_smem_get_global()
498 for (i = 0; i < smem->num_regions; i++) { in qcom_smem_get_global()
499 region = &smem->regions[i]; in qcom_smem_get_global()
511 static void *qcom_smem_get_private(struct qcom_smem *smem, in qcom_smem_get_private() argument
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/cuda/
H A Dvec_distance.hpp70 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(int* smem, int tid) in reduceAll()
72 reduce<THREAD_DIM>(smem, mySum, tid, plus<int>()); in reduceAll()
94 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(float* smem, int tid) in reduceAll()
96 reduce<THREAD_DIM>(smem, mySum, tid, plus<float>()); in reduceAll()
120 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(float* smem, int tid) in reduceAll()
122 reduce<THREAD_DIM>(smem, mySum, tid, plus<float>()); in reduceAll()
145 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(int* smem, int tid) in reduceAll()
147 reduce<THREAD_DIM>(smem, mySum, tid, plus<int>()); in reduceAll()
160 …bal(const T1* vec1, const T2* vec2, int len, Dist& dist, typename Dist::result_type* smem, int tid) in calcVecDiffGlobal() argument
173 dist.reduceAll<THREAD_DIM>(smem, tid); in calcVecDiffGlobal()
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/cuda/
H A Dvec_distance.hpp70 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(int* smem, int tid) in reduceAll()
72 reduce<THREAD_DIM>(smem, mySum, tid, plus<int>()); in reduceAll()
94 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(float* smem, int tid) in reduceAll()
96 reduce<THREAD_DIM>(smem, mySum, tid, plus<float>()); in reduceAll()
120 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(float* smem, int tid) in reduceAll()
122 reduce<THREAD_DIM>(smem, mySum, tid, plus<float>()); in reduceAll()
145 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(int* smem, int tid) in reduceAll()
147 reduce<THREAD_DIM>(smem, mySum, tid, plus<int>()); in reduceAll()
160 …bal(const T1* vec1, const T2* vec2, int len, Dist& dist, typename Dist::result_type* smem, int tid) in calcVecDiffGlobal() argument
173 dist.reduceAll<THREAD_DIM>(smem, tid); in calcVecDiffGlobal()
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/cuda/
H A Dvec_distance.hpp70 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(int* smem, int tid) in reduceAll()
72 reduce<THREAD_DIM>(smem, mySum, tid, plus<int>()); in reduceAll()
94 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(float* smem, int tid) in reduceAll()
96 reduce<THREAD_DIM>(smem, mySum, tid, plus<float>()); in reduceAll()
120 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(float* smem, int tid) in reduceAll()
122 reduce<THREAD_DIM>(smem, mySum, tid, plus<float>()); in reduceAll()
145 template <int THREAD_DIM> __device__ __forceinline__ void reduceAll(int* smem, int tid) in reduceAll()
147 reduce<THREAD_DIM>(smem, mySum, tid, plus<int>()); in reduceAll()
160 …bal(const T1* vec1, const T2* vec2, int len, Dist& dist, typename Dist::result_type* smem, int tid) in calcVecDiffGlobal() argument
173 dist.reduceAll<THREAD_DIM>(smem, tid); in calcVecDiffGlobal()
[all …]
/OK3568_Linux_fs/yocto/meta-openembedded/meta-oe/dynamic-layers/meta-python/recipes-support/smem/smem/
H A D0001-smem-fix-support-for-source-option-python3.patch4 Subject: [PATCH] smem: fix support for --source option (python3)
11 File "./smem", line 727, in <module>
13 File "./smem", line 299, in showpids
15 File "./smem", line 519, in showtable
17 File "./smem", line 118, in totalmem
19 File "./smem", line 193, in memory
32 smem | 4 ++--
35 diff --git a/smem b/smem
37 --- a/smem
38 +++ b/smem
/OK3568_Linux_fs/yocto/meta-openembedded/meta-oe/dynamic-layers/meta-python/recipes-support/smem/
H A Dsmem_1.5.bb2 DESCRIPTION = "smem is a tool that can give numerous reports on memory usage on Linux \
3 systems. Unlike existing tools, smem can report proportional set size (PSS), \
6 HOMEPAGE = "http://www.selenic.com/smem/"
14 file://0001-smem-fix-support-for-source-option-python3.patch"
18 UPSTREAM_CHECK_URI = "https://selenic.com/repo/smem/tags"
30 install -m 0755 ${S}/smem ${D}${bindir}/
31 sed -i -e '1s,#!.*python.*,#!${USRBINPATH}/env python3,' ${D}${bindir}/smem
33 install -m 0644 ${S}/smem.8 ${D}/${mandir}/man8/
/OK3568_Linux_fs/u-boot/lib/
H A Dsysmem.c170 struct memblock *smem; in sysmem_overflow_check() local
220 smem = list_entry(node, struct memblock, node); in sysmem_overflow_check()
226 if (sysmem_is_overlap(smem->base, smem->size, in sysmem_overflow_check()
228 if (smem->attr.flags & F_KMEM_CAN_OVERLAP) in sysmem_overflow_check()
236 smem->attr.name, (ulong)smem->base, in sysmem_overflow_check()
237 (ulong)(smem->base + smem->size)); in sysmem_overflow_check()
244 if (smem->attr.flags & F_OFC) { in sysmem_overflow_check()
246 (smem->base + smem->size - sizeof(*check)); in sysmem_overflow_check()
248 } else if (smem->attr.flags & F_HOFC) { in sysmem_overflow_check()
250 (smem->base - sizeof(*check)); in sysmem_overflow_check()
/OK3568_Linux_fs/kernel/Documentation/devicetree/bindings/soc/qcom/
H A Dqcom,smem.txt10 "qcom,smem"
37 smem_region: smem@fa00000 {
43 smem@fa00000 {
44 compatible = "qcom,smem";
H A Dqcom,smp2p.txt35 - qcom,smem:
38 Definition: two identifiers of the inbound and outbound smem items used
77 - #qcom,smem-state-cells:
89 qcom,smem = <431>, <451>;
101 #qcom,smem-state-cells = <1>;
H A Dqcom,wcnss.txt64 - qcom,smem-state:
69 - qcom,smem-state-names:
110 qcom,smem-state = <&apps_smsm 10>, <&apps_smsm 9>;
111 qcom,smem-state-names = "tx-enable", "tx-rings-empty";
/OK3568_Linux_fs/kernel/Documentation/devicetree/bindings/remoteproc/
H A Dqcom,adsp.txt131 - qcom,smem-states:
134 Definition: reference to the smem state for requesting the ADSP to
137 - qcom,smem-state-names:
175 qcom,smem-states = <&adsp_smp2p_out 0>;
176 qcom,smem-state-names = "stop";
210 qcom,smem-states = <&slpi_smp2p_out 0>;
211 qcom,smem-state-names = "stop";
H A Dqcom,hexagon-v56.txt83 - qcom,smem-states:
86 Definition: reference to the smem state for requesting the Hexagon to
89 - qcom,smem-state-names:
138 qcom,smem-states = <&adsp_smp2p_out 0>;
139 qcom,smem-state-names = "stop";
H A Dqcom,wcnss-pil.txt45 - qcom,smem-states:
51 - qcom,smem-state-names:
118 qcom,smem-states = <&wcnss_smp2p_out 0>;
119 qcom,smem-state-names = "stop";
/OK3568_Linux_fs/kernel/drivers/video/fbdev/
H A Dpmagb-b-fb.c38 volatile void __iomem *smem; member
301 par->smem = ioremap(info->fix.smem_start, info->fix.smem_len); in pmagbbfb_probe()
302 if (!par->smem) { in pmagbbfb_probe()
308 info->screen_base = (void __iomem *)par->smem + vid_base * 0x1000; in pmagbbfb_probe()
338 iounmap(par->smem); in pmagbbfb_probe()
363 iounmap(par->smem); in pmagbbfb_remove()
/OK3568_Linux_fs/kernel/arch/arm/boot/dts/
H A Dqcom-msm8974.dtsi49 smem_region: smem@fa00000 {
361 qcom,smem-states = <&adsp_smp2p_out 0>;
362 qcom,smem-state-names = "stop";
374 smem {
375 compatible = "qcom,smem";
385 qcom,smem = <443>, <429>;
397 #qcom,smem-state-cells = <1>;
410 qcom,smem = <435>, <428>;
422 #qcom,smem-state-cells = <1>;
435 qcom,smem = <451>, <431>;
[all …]
/OK3568_Linux_fs/buildroot/package/rpi-userland/
H A D0003-Disable-Werror-everywhere.patch25 host_applications/linux/apps/smem/CMakeLists.txt | 2 +-
72 diff --git a/host_applications/linux/apps/smem/CMakeLists.txt b/host_applications/linux/apps/smem/C…
74 --- a/host_applications/linux/apps/smem/CMakeLists.txt
75 +++ b/host_applications/linux/apps/smem/CMakeLists.txt
/OK3568_Linux_fs/kernel/arch/arm64/boot/dts/qcom/
H A Dsm8150.dtsi302 smem {
303 compatible = "qcom,smem";
310 qcom,smem = <94>, <432>;
321 #qcom,smem-state-cells = <1>;
334 qcom,smem = <443>, <429>;
345 #qcom,smem-state-cells = <1>;
358 qcom,smem = <435>, <428>;
369 #qcom,smem-state-cells = <1>;
382 qcom,smem = <481>, <430>;
393 #qcom,smem-state-cells = <1>;
[all …]
H A Dipq6018.dtsi175 smem {
176 compatible = "qcom,smem";
468 qcom,smem-states = <&wcss_smp2p_out 0>,
470 qcom,smem-state-names = "shutdown",
490 qcom,smem = <435>, <428>;
502 #qcom,smem-state-cells = <1>;
H A Dqcs404.dtsi289 smem {
290 compatible = "qcom,smem";
516 qcom,smem-states = <&cdsp_smp2p_out 0>;
517 qcom,smem-state-names = "stop";
757 qcom,smem-states = <&wcss_smp2p_out 0>;
758 qcom,smem-state-names = "stop";
1262 qcom,smem-states = <&adsp_smp2p_out 0>;
1263 qcom,smem-state-names = "stop";
1338 qcom,smem = <443>, <429>;
1346 #qcom,smem-state-cells = <1>;
[all …]

123