|
|
|
|
#include <stdio.h>
|
|
|
|
|
#include <memory.h>
|
|
|
|
|
#include <string.h>
|
|
|
|
|
|
|
|
|
|
#include <map>
|
|
|
|
|
|
|
|
|
|
#ifndef _WIN32
|
|
|
|
|
#include <unistd.h>
|
|
|
|
|
#endif
|
|
|
|
|
|
|
|
|
|
// include thrust
|
|
|
|
|
#include <thrust/version.h>
|
|
|
|
|
#include <thrust/remove.h>
|
|
|
|
|
#include <thrust/device_vector.h>
|
|
|
|
|
#include <thrust/iterator/constant_iterator.h>
|
|
|
|
|
|
|
|
|
|
#include "miner.h"
|
|
|
|
|
|
|
|
|
|
#include "cuda_helper.h"
|
|
|
|
|
|
|
|
|
|
extern char *device_name[8];
|
|
|
|
|
|
|
|
|
|
// CUDA Devices on the System
|
|
|
|
|
extern "C" int cuda_num_devices()
|
|
|
|
|
{
|
|
|
|
|
int version;
|
|
|
|
|
cudaError_t err = cudaDriverGetVersion(&version);
|
|
|
|
|
if (err != cudaSuccess)
|
|
|
|
|
{
|
|
|
|
|
applog(LOG_ERR, "Unable to query CUDA driver version! Is an nVidia driver installed?");
|
|
|
|
|
exit(1);
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
int maj = version / 1000, min = version % 100; // same as in deviceQuery sample
|
|
|
|
|
if (maj < 5 || (maj == 5 && min < 5))
|
|
|
|
|
{
|
|
|
|
|
applog(LOG_ERR, "Driver does not support CUDA %d.%d API! Update your nVidia driver!", 5, 5);
|
|
|
|
|
exit(1);
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
int GPU_N;
|
|
|
|
|
err = cudaGetDeviceCount(&GPU_N);
|
|
|
|
|
if (err != cudaSuccess)
|
|
|
|
|
{
|
|
|
|
|
applog(LOG_ERR, "Unable to query number of CUDA devices! Is an nVidia driver installed?");
|
|
|
|
|
exit(1);
|
|
|
|
|
}
|
|
|
|
|
return GPU_N;
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
extern "C" void cuda_devicenames()
|
|
|
|
|
{
|
|
|
|
|
cudaError_t err;
|
|
|
|
|
int GPU_N;
|
|
|
|
|
err = cudaGetDeviceCount(&GPU_N);
|
|
|
|
|
if (err != cudaSuccess)
|
|
|
|
|
{
|
|
|
|
|
applog(LOG_ERR, "Unable to query number of CUDA devices! Is an nVidia driver installed?");
|
|
|
|
|
exit(1);
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
for (int i=0; i < GPU_N; i++)
|
|
|
|
|
{
|
|
|
|
|
cudaDeviceProp props;
|
|
|
|
|
cudaGetDeviceProperties(&props, device_map[i]);
|
|
|
|
|
|
|
|
|
|
device_name[i] = strdup(props.name);
|
|
|
|
|
device_sm[i] = props.major * 100 + props.minor * 10;
|
|
|
|
|
}
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
// Can't be called directly in cpu-miner.c
|
|
|
|
|
extern "C" void cuda_devicereset()
|
|
|
|
|
{
|
|
|
|
|
cudaDeviceReset();
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
static bool substringsearch(const char *haystack, const char *needle, int &match)
|
|
|
|
|
{
|
|
|
|
|
int hlen = (int) strlen(haystack);
|
|
|
|
|
int nlen = (int) strlen(needle);
|
|
|
|
|
for (int i=0; i < hlen; ++i)
|
|
|
|
|
{
|
|
|
|
|
if (haystack[i] == ' ') continue;
|
|
|
|
|
int j=0, x = 0;
|
|
|
|
|
while(j < nlen)
|
|
|
|
|
{
|
|
|
|
|
if (haystack[i+x] == ' ') {++x; continue;}
|
|
|
|
|
if (needle[j] == ' ') {++j; continue;}
|
|
|
|
|
if (needle[j] == '#') return ++match == needle[j+1]-'0';
|
|
|
|
|
if (tolower(haystack[i+x]) != tolower(needle[j])) break;
|
|
|
|
|
++j; ++x;
|
|
|
|
|
}
|
|
|
|
|
if (j == nlen) return true;
|
|
|
|
|
}
|
|
|
|
|
return false;
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
// CUDA Gerät nach Namen finden (gibt Geräte-Index zurück oder -1)
|
|
|
|
|
extern "C" int cuda_finddevice(char *name)
|
|
|
|
|
{
|
|
|
|
|
int num = cuda_num_devices();
|
|
|
|
|
int match = 0;
|
|
|
|
|
for (int i=0; i < num; ++i)
|
|
|
|
|
{
|
|
|
|
|
cudaDeviceProp props;
|
|
|
|
|
if (cudaGetDeviceProperties(&props, i) == cudaSuccess)
|
|
|
|
|
if (substringsearch(props.name, name, match)) return i;
|
|
|
|
|
}
|
|
|
|
|
return -1;
|
|
|
|
|
}
|
|
|
|
|
|
|
|
|
|
// Zeitsynchronisations-Routine von cudaminer mit CPU sleep
|
|
|
|
|
typedef struct { double value[8]; } tsumarray;
|
|
|
|
|
cudaError_t MyStreamSynchronize(cudaStream_t stream, int situation, int thr_id)
|
|
|
|
|
{
|
|
|
|
|
cudaError_t result = cudaSuccess;
|
|
|
|
|
if (situation >= 0)
|
|
|
|
|
{
|
|
|
|
|
static std::map<int, tsumarray> tsum;
|
|
|
|
|
|
|
|
|
|
double a = 0.95, b = 0.05;
|
|
|
|
|
if (tsum.find(situation) == tsum.end()) { a = 0.5; b = 0.5; } // faster initial convergence
|
|
|
|
|
|
|
|
|
|
double tsync = 0.0;
|
|
|
|
|
double tsleep = 0.95 * tsum[situation].value[thr_id];
|
|
|
|
|
if (cudaStreamQuery(stream) == cudaErrorNotReady)
|
|
|
|
|
{
|
|
|
|
|
usleep((useconds_t)(1e6*tsleep));
|
|
|
|
|
struct timeval tv_start, tv_end;
|
|
|
|
|
gettimeofday(&tv_start, NULL);
|
|
|
|
|
result = cudaStreamSynchronize(stream);
|
|
|
|
|
gettimeofday(&tv_end, NULL);
|
|
|
|
|
tsync = 1e-6 * (tv_end.tv_usec-tv_start.tv_usec) + (tv_end.tv_sec-tv_start.tv_sec);
|
|
|
|
|
}
|
|
|
|
|
if (tsync >= 0) tsum[situation].value[thr_id] = a * tsum[situation].value[thr_id] + b * (tsleep+tsync);
|
|
|
|
|
}
|
|
|
|
|
else
|
|
|
|
|
result = cudaStreamSynchronize(stream);
|
|
|
|
|
return result;
|
|
|
|
|
}
|