Home
last modified time | relevance | path

Searched refs:filter_ptr (Results 1 – 25 of 35) sorted by relevance

12

/external/tensorflow/tensorflow/lite/kernels/internal/optimized/integer_ops/
Ddepthwise_conv_hybrid_3x3_filter.h131 const int8* filter_ptr, const float* bias_ptr,
1022 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
1065 const int8* filter_ptr, const float* bias_ptr,
2029 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
2073 const int8* filter_ptr, const float* bias_ptr,
2166 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
2189 const int8* filter_ptr, const float* bias_ptr,
2335 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
2359 const int8* filter_ptr, const float* bias_ptr,
2539 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
[all …]
Ddepthwise_conv_3x3_filter.h114 const int8* filter_ptr, const int32* bias_ptr,
925 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
969 const int8* filter_ptr, const int32* bias_ptr,
1886 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
1931 const int8* filter_ptr, const int32* bias_ptr,
2018 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
2043 const int8* filter_ptr, const int32* bias_ptr,
2182 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
2207 const int8* filter_ptr, const int32* bias_ptr,
2379 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
[all …]
Ddepthwise_conv.h50 int input_ptr_increment, const int8* filter_ptr,
54 filter_s8.val[0] = vld1_s8(filter_ptr);
55 filter_s8.val[1] = vld1_s8(filter_ptr + 8);
96 int input_ptr_increment, const int8* filter_ptr,
99 const int8x8_t filter_s8 = vld1_s8(filter_ptr);
163 int input_ptr_increment, const int8* filter_ptr,
166 const int8x8_t filter_s8 = vld1_s8(filter_ptr);
231 int input_ptr_increment, const int8* filter_ptr,
236 const int8x8_t filter_s8 = vld1_s8(filter_ptr + 8 * i);
305 int input_ptr_increment, const int8* filter_ptr,
[all …]
/external/tensorflow/tensorflow/lite/kernels/internal/optimized/
Ddepthwiseconv_float.h38 const float* filter_ptr, float* acc_buffer_ptr) {
42 filter[i] = vld1q_f32(filter_ptr + 4 * i);
99 const float* filter_ptr, float* acc_buffer_ptr) {
100 const float32x2_t filters = vld1_f32(filter_ptr);
182 const float* filter_ptr, float* acc_buffer_ptr) {
185 const float* local_filter_ptr = filter_ptr;
253 const float* filter_ptr, float* acc_buffer_ptr) {
256 const float* local_filter_ptr = filter_ptr;
323 const float* filter_ptr, float* acc_buffer_ptr) {
326 const float* local_filter_ptr = filter_ptr;
[all …]
Ddepthwiseconv_uint8.h45 int input_ptr_increment, const uint8* filter_ptr,
49 filter_u8.val[0] = vld1_u8(filter_ptr);
50 filter_u8.val[1] = vld1_u8(filter_ptr + 8);
92 int input_ptr_increment, const uint8* filter_ptr,
95 const uint8x8_t filter_u8 = vld1_u8(filter_ptr);
160 int input_ptr_increment, const uint8* filter_ptr,
163 const uint8x8_t filter_u8 = vld1_u8(filter_ptr);
230 int input_ptr_increment, const uint8* filter_ptr,
235 const uint8x8_t filter_u8 = vld1_u8(filter_ptr + 8 * i);
307 int input_ptr_increment, const uint8* filter_ptr,
[all …]
Ddepthwiseconv_uint8_3x3_filter.h323 static inline void Run(const uint8* input_ptr, const uint8* filter_ptr,
1216 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
1256 static inline void Run(const uint8* input_ptr, const uint8* filter_ptr,
2041 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
2081 static inline void Run(const uint8* input_ptr, const uint8* filter_ptr,
3073 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
3113 static inline void Run(const uint8* input_ptr, const uint8* filter_ptr,
3995 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
4036 static inline void Run(const uint8* input_ptr, const uint8* filter_ptr,
4128 [filter_ptr] "+r"(filter_ptr), [input_ptr] "+r"(input_ptr),
[all …]
Dlegacy_optimized_ops.h809 const uint8* filter_ptr = filter_data + in + out * input_size; in LegacyFullyConnectedAsGEMVWorkerImpl() local
810 uint8x16_t filter_val_u8_0 = vld1q_u8(filter_ptr); in LegacyFullyConnectedAsGEMVWorkerImpl()
811 optimized_ops_preload_l1_stream(filter_ptr + 64); in LegacyFullyConnectedAsGEMVWorkerImpl()
812 filter_ptr += input_size; in LegacyFullyConnectedAsGEMVWorkerImpl()
813 uint8x16_t filter_val_u8_1 = vld1q_u8(filter_ptr); in LegacyFullyConnectedAsGEMVWorkerImpl()
814 optimized_ops_preload_l1_stream(filter_ptr + 64); in LegacyFullyConnectedAsGEMVWorkerImpl()
815 filter_ptr += input_size; in LegacyFullyConnectedAsGEMVWorkerImpl()
816 uint8x16_t filter_val_u8_2 = vld1q_u8(filter_ptr); in LegacyFullyConnectedAsGEMVWorkerImpl()
817 optimized_ops_preload_l1_stream(filter_ptr + 64); in LegacyFullyConnectedAsGEMVWorkerImpl()
818 filter_ptr += input_size; in LegacyFullyConnectedAsGEMVWorkerImpl()
[all …]
/external/tensorflow/tensorflow/core/kernels/
Dconv_ops_gpu.cc117 se::DeviceMemory<T> input_ptr, se::DeviceMemory<T> filter_ptr, in AutotuneFusedConv() argument
149 return (*runner)(stream, profile_result, scratch, input_ptr, filter_ptr, in AutotuneFusedConv()
159 se::dnn::ToDataType<T>::value, input_ptr, filter_ptr, output_ptr, in AutotuneFusedConv()
200 se::dnn::ToDataType<T>::value, input_ptr, filter_ptr, output_ptr, in AutotuneFusedConv()
232 se::DeviceMemory<double> input_ptr, se::DeviceMemory<double> filter_ptr,
248 se::DeviceMemory<float> input_ptr, se::DeviceMemory<float> filter_ptr,
266 se::DeviceMemory<Eigen::half> filter_ptr,
278 se::DeviceMemory<T> filter_ptr, in AutotuneUnfusedConv() argument
308 filter_ptr = se::DeviceMemory<T>( in AutotuneUnfusedConv()
309 WrapRedzoneBestEffort(&rz_allocator, filter_ptr)); in AutotuneUnfusedConv()
[all …]
Dconv_ops_gpu.h112 se::DeviceMemory<T> input_ptr, se::DeviceMemory<T> filter_ptr,
123 se::DeviceMemory<T> filter_ptr,
167 se::DeviceMemory<T> filter_ptr, in LaunchAutotunedConv() argument
193 filter_ptr, out_ptr); in LaunchAutotunedConv()
196 kind, input_desc, in_ptr, filter_desc, filter_ptr, output_desc, out_ptr, in LaunchAutotunedConv()
Ddilation_ops_gpu.cu.cc40 const T* __restrict__ filter_ptr, int batch, int input_rows, int input_cols, in DilationKernel() argument
64 filter_ptr[d + depth * (w + filter_cols * h)]; in DilationKernel()
79 const T* __restrict__ filter_ptr, const T* __restrict__ out_backprop_ptr, in DilationBackpropInputKernel() argument
109 filter_ptr[d + depth * (w + filter_cols * h)]; in DilationBackpropInputKernel()
129 const T* __restrict__ filter_ptr, const T* __restrict__ out_backprop_ptr, in DilationBackpropFilterKernel() argument
159 filter_ptr[d + depth * (w + filter_cols * h)]; in DilationBackpropFilterKernel()
Dconv_ops.cc410 auto filter_ptr = filter.template flat<float>().data(); in Run() local
413 functor::DeepConv2D<CPUDevice, float>()(ctx, args, input_ptr, filter_ptr, in Run()
477 auto filter_ptr = filter.template flat<float>().data(); in Run() local
481 ctx, desc, input_ptr, filter_ptr, output_ptr); in Run()
1104 auto filter_ptr = in operator ()() local
1137 filter_ptr, conv_desc, output_desc, output_ptr, ConvolveScratchSize); in operator ()()
1144 stream, input_desc, input_ptr, filter_desc, filter_ptr, conv_desc, in operator ()()
Dconv_grad_input_ops.cc345 auto filter_ptr = in operator ()() local
381 filter_desc, filter_ptr, conv_desc, output_desc, out_backprop_ptr, in operator ()()
390 input_desc, in_backprop_ptr, filter_desc, filter_ptr, in operator ()()
Dconv_ops_fused_impl.h572 se::DeviceMemory<T> filter_ptr = tensor_on_device(transformed_filter);
615 kSideInputScale, leakyrelu_alpha, input_ptr, filter_ptr, output_ptr,
658 input_ptr, filter_ptr, side_input_ptr, bias_ptr, output_ptr);
663 filter_desc, filter_ptr, // filter
Dconv_ops_3d.cc477 auto filter_ptr = in launch() local
509 filter_ptr, conv_desc, output_desc, output_ptr, ConvolveScratchSize); in launch()
516 stream, input_desc, input_ptr, filter_desc, filter_ptr, conv_desc, in launch()
Ddepthwise_conv_op_gpu.h301 const S* filter_ptr = filter_read_offset + shared_data;
305 filter_ptr -= kBlockDepth;
307 const S filter_value = *filter_ptr;
313 filter_ptr += kBlockDepth;
594 const S* filter_ptr = filter_read_offset + shared_data;
598 filter_ptr -= kBlockDepth;
600 const S filter_value = *filter_ptr;
606 filter_ptr += kBlockDepth;
/external/trace-cmd/lib/trace-cmd/
Dtrace-filter.c126 struct filter ***filter_ptr; in tracecmd_filter_add() local
156 filter_ptr = &trace_filter->event_notrace; in tracecmd_filter_add()
159 filter_ptr = &trace_filter->event_filters; in tracecmd_filter_add()
163 filters = realloc(*filter_ptr, sizeof(*filters) * (*nr + 1)); in tracecmd_filter_add()
167 *filter_ptr = filters; in tracecmd_filter_add()
/external/libaom/av1/common/
Dfilter.h106 const int16_t *filter_ptr; member
259 ? av1_interp_4tap[BILINEAR].filter_ptr in av1_get_interp_filter_kernel()
261 ? av1_interp_4tap[interp_filter].filter_ptr in av1_get_interp_filter_kernel()
262 : av1_interp_filter_params_list[interp_filter].filter_ptr); in av1_get_interp_filter_kernel()
267 return filter_params->filter_ptr + filter_params->taps * subpel; in av1_get_interp_filter_subpel_kernel()
/external/libaom/av1/common/arm/
Dav1_convolve_scale_neon_i8mm.c334 im_h, filter_params_x->filter_ptr, subpel_x_qn, x_step_qn); in av1_convolve_2d_scale_neon_i8mm()
343 const int16_t *x_filter = filter_params_x->filter_ptr + filter_offset; in av1_convolve_2d_scale_neon_i8mm()
362 filter_params_y->filter_ptr, conv_params, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_i8mm()
366 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_i8mm()
371 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_i8mm()
375 filter_params_y->filter_ptr, subpel_y_qn, in av1_convolve_2d_scale_neon_i8mm()
384 dst16_stride, w, h, filter_params_y->filter_ptr, conv_params, in av1_convolve_2d_scale_neon_i8mm()
389 dst16_stride, w, h, filter_params_y->filter_ptr, subpel_y_qn, in av1_convolve_2d_scale_neon_i8mm()
395 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_i8mm()
400 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_i8mm()
Dav1_convolve_scale_neon_dotprod.c358 im_h, filter_params_x->filter_ptr, subpel_x_qn, x_step_qn); in av1_convolve_2d_scale_neon_dotprod()
367 const int16_t *x_filter = filter_params_x->filter_ptr + filter_offset; in av1_convolve_2d_scale_neon_dotprod()
386 filter_params_y->filter_ptr, conv_params, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_dotprod()
390 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_dotprod()
395 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_dotprod()
399 filter_params_y->filter_ptr, subpel_y_qn, in av1_convolve_2d_scale_neon_dotprod()
408 dst16_stride, w, h, filter_params_y->filter_ptr, conv_params, in av1_convolve_2d_scale_neon_dotprod()
413 dst16_stride, w, h, filter_params_y->filter_ptr, subpel_y_qn, in av1_convolve_2d_scale_neon_dotprod()
419 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_dotprod()
424 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon_dotprod()
Dresize_neon_i8mm.c98 const int16_t *const filter_ptr, in scale_plane_2_to_1_6tap() argument
107 const int16x8_t filters = vshrq_n_s16(vld1q_s16(filter_ptr), 1); in scale_plane_2_to_1_6tap()
181 const int16_t *const filter_ptr, in scale_plane_4_to_1_8tap() argument
189 const int16x8_t filters = vshrq_n_s16(vld1q_s16(filter_ptr), 1); in scale_plane_4_to_1_8tap()
257 .filter_ptr; in av1_resize_and_extend_frame_neon_i8mm()
273 .filter_ptr; in av1_resize_and_extend_frame_neon_i8mm()
Dresize_neon_dotprod.c110 const int16_t *const filter_ptr, in scale_plane_2_to_1_8tap() argument
119 const int16x8_t filters = vshrq_n_s16(vld1q_s16(filter_ptr), 1); in scale_plane_2_to_1_8tap()
208 const int16_t *const filter_ptr, in scale_plane_4_to_1_8tap() argument
216 const int16x8_t filters = vshrq_n_s16(vld1q_s16(filter_ptr), 1); in scale_plane_4_to_1_8tap()
285 .filter_ptr; in av1_resize_and_extend_frame_neon_dotprod()
301 .filter_ptr; in av1_resize_and_extend_frame_neon_dotprod()
Dav1_convolve_scale_neon.c668 im_h, filter_params_x->filter_ptr, subpel_x_qn, x_step_qn); in av1_convolve_2d_scale_neon()
672 im_h, filter_params_x->filter_ptr, subpel_x_qn, x_step_qn); in av1_convolve_2d_scale_neon()
682 const int16_t *x_filter = filter_params_x->filter_ptr + filter_offset; in av1_convolve_2d_scale_neon()
707 filter_params_y->filter_ptr, conv_params, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon()
711 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon()
716 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon()
720 filter_params_y->filter_ptr, subpel_y_qn, in av1_convolve_2d_scale_neon()
729 dst16_stride, w, h, filter_params_y->filter_ptr, conv_params, in av1_convolve_2d_scale_neon()
734 dst16_stride, w, h, filter_params_y->filter_ptr, subpel_y_qn, in av1_convolve_2d_scale_neon()
740 filter_params_y->filter_ptr, subpel_y_qn, y_step_qn); in av1_convolve_2d_scale_neon()
[all …]
Dresize_neon.c244 const int16_t *const filter_ptr, in scale_plane_2_to_1_6tap() argument
252 const int16x8_t filters = vshrq_n_s16(vld1q_s16(filter_ptr), 1); in scale_plane_2_to_1_6tap()
325 const int16_t *const filter_ptr, in scale_plane_4_to_1_6tap() argument
332 const int16x8_t filters = vshrq_n_s16(vld1q_s16(filter_ptr), 1); in scale_plane_4_to_1_6tap()
385 (const InterpKernel *)av1_interp_filter_params_list[BILINEAR].filter_ptr; in scale_plane_4_to_3_bilinear()
750 .filter_ptr; in av1_resize_and_extend_frame_neon()
778 .filter_ptr; in av1_resize_and_extend_frame_neon()
802 .filter_ptr; in av1_resize_and_extend_frame_neon()
/external/tensorflow/tensorflow/lite/kernels/
Dcpu_backend_gemm_custom_gemv.h337 const LhsScalar* filter_ptr = lhs_data + row * lhs_params.cols;
370 const LhsScalar* local_filter_ptr = filter_ptr;
392 filter_ptr += 16;
431 filter_ptr + 0 * lhs_params.cols, lhs_params.zero_point);
433 filter_ptr + 1 * lhs_params.cols, lhs_params.zero_point);
435 filter_ptr + 2 * lhs_params.cols, lhs_params.zero_point);
437 filter_ptr + 3 * lhs_params.cols, lhs_params.zero_point);
438 filter_ptr += 8;
472 const LhsScalar* local_filter_ptr = filter_ptr - back;
473 filter_ptr += lhs_params.cols - in;
[all …]
/external/grpc-grpc/test/core/filters/
Dfilter_test.h124 ChannelFilter* filter_ptr() { return impl_->filter.get(); } in filter_ptr() function
224 Filter* filter() { return static_cast<Filter*>(filter_ptr()); } in filter()

12