From ae43c2bc32fbb838bfebeeaf2c2b058ccab5c83c Mon Sep 17 00:00:00 2001
From: Joseph Redmon <pjreddie@burninator.cs.washington.edu>
Date: Thu, 23 Jun 2016 05:31:14 +0000
Subject: [PATCH] hi
---
src/dropout_layer_kernels.cu | 16 +++++++++++++---
1 files changed, 13 insertions(+), 3 deletions(-)
diff --git a/src/dropout_layer_kernels.cu b/src/dropout_layer_kernels.cu
index 4561d89..7e51bd5 100644
--- a/src/dropout_layer_kernels.cu
+++ b/src/dropout_layer_kernels.cu
@@ -1,8 +1,11 @@
+#include "cuda_runtime.h"
+#include "curand.h"
+#include "cublas_v2.h"
+
extern "C" {
#include "dropout_layer.h"
#include "cuda.h"
#include "utils.h"
-#include "params.h"
}
__global__ void yoloswag420blazeit360noscope(float *input, int size, float *rand, float prob, float scale)
@@ -11,17 +14,24 @@
if(id < size) input[id] = (rand[id] < prob) ? 0 : input[id]*scale;
}
-extern "C" void forward_dropout_layer_gpu(dropout_layer layer, network_state state)
+void forward_dropout_layer_gpu(dropout_layer layer, network_state state)
{
if (!state.train) return;
int size = layer.inputs*layer.batch;
cuda_random(layer.rand_gpu, size);
+ /*
+ int i;
+ for(i = 0; i < size; ++i){
+ layer.rand[i] = rand_uniform();
+ }
+ cuda_push_array(layer.rand_gpu, layer.rand, size);
+ */
yoloswag420blazeit360noscope<<<cuda_gridsize(size), BLOCK>>>(state.input, size, layer.rand_gpu, layer.probability, layer.scale);
check_error(cudaPeekAtLastError());
}
-extern "C" void backward_dropout_layer_gpu(dropout_layer layer, network_state state)
+void backward_dropout_layer_gpu(dropout_layer layer, network_state state)
{
if(!state.delta) return;
int size = layer.inputs*layer.batch;
--
Gitblit v1.10.0