 }
 
 template <typename T>
-__global__ void RenormGradKernelFunc2(T* x_data, T* dout_data, T* dx_data,
-                                      int64_t size, T* dim_value,
+__global__ void RenormGradKernelFunc2(const T* x_data, const T* dout_data,
+                                      T* dx_data, int64_t size, T* dim_value,
                                       T* dim_power_sum, T* weight_derivative,
                                       int64_t dimension_each, float p,
                                       float max_norm, int64_t dim_divisor) {

}

template <typename T>
__global__ void RenormKernelFunc4(T* x_data, T* out_data, int64_t size,
                                  T* dim_value, int64_t dimension_each,
                                  int64_t dim_divisor) {
  int64_t i = ((int64_t)blockIdx.x) * blockDim.x + threadIdx.x;

                        ops::CUDARenormKernel<double>);

REGISTER_OP_CUDA_KERNEL(renorm_grad, ops::CUDAGradRenormKernel<float>,
                        ops::CUDAGradRenormKernel<double>);
