Commit 5f2c3151b474ac49635701ff3f56966c23abfd57
2011-07-30T16:33:43
Read buffers only after reading data back now that we're sync.
1 2 3 4 5 6 7 8 9 10 11 12 13 14 15 16 17 18 19 20 21 22 23 24 25 26 27 28 29 30 31 32 33 34 35 36 37 38 39 40 41 42 43 44
diff --git a/main.c b/main.c
index abde75a..53d0a29 100644
--- a/main.c
+++ b/main.c
@@ -3059,19 +3059,6 @@ static void *gpuminer_thread(void *userdata)
if (unlikely(status != CL_SUCCESS))
{ applog(LOG_ERR, "Error: clSetKernelArg of all params failed."); goto out; }
- /* MAXBUFFERS entry is used as a flag to say nonces exist */
- if (res[MAXBUFFERS]) {
- /* Clear the buffer again */
- status = clEnqueueWriteBuffer(clState->commandQueue, clState->outputBuffer, CL_TRUE, 0,
- BUFFERSIZE, blank_res, 0, NULL, NULL);
- if (unlikely(status != CL_SUCCESS))
- { applog(LOG_ERR, "Error: clEnqueueWriteBuffer failed."); goto out; }
- if (opt_debug)
- applog(LOG_DEBUG, "GPU %d found something?", gpu);
- postcalc_hash_async(mythr, work, res);
- memset(res, 0, BUFFERSIZE);
- }
-
status = clEnqueueNDRangeKernel(clState->commandQueue, *kernel, 1, NULL,
globalThreads, localThreads, 0, NULL, NULL);
if (unlikely(status != CL_SUCCESS))
@@ -3103,6 +3090,19 @@ static void *gpuminer_thread(void *userdata)
}
set_threads_hashes(vectors, &threads, &hashes, globalThreads, localThreads[0]);
+ /* MAXBUFFERS entry is used as a flag to say nonces exist */
+ if (res[MAXBUFFERS]) {
+ /* Clear the buffer again */
+ status = clEnqueueWriteBuffer(clState->commandQueue, clState->outputBuffer, CL_TRUE, 0,
+ BUFFERSIZE, blank_res, 0, NULL, NULL);
+ if (unlikely(status != CL_SUCCESS))
+ { applog(LOG_ERR, "Error: clEnqueueWriteBuffer failed."); goto out; }
+ if (opt_debug)
+ applog(LOG_DEBUG, "GPU %d found something?", gpu);
+ postcalc_hash_async(mythr, work, res);
+ memset(res, 0, BUFFERSIZE);
+ }
+
gettimeofday(&tv_end, NULL);
timeval_subtract(&diff, &tv_end, &tv_start);
hashes_done += hashes;