71 lines
1.2 KiB
C
71 lines
1.2 KiB
C
#define _GNU_SOURCE /* See feature_test_macros(7) */
|
|
#include <stdio.h>
|
|
#include <unistd.h>
|
|
#include <stdlib.h>
|
|
#include <stdint.h>
|
|
#include <sys/syscall.h> /* For SYS_xxx definitions */
|
|
#include <sched.h>
|
|
#include <sys/types.h>
|
|
#include <sys/stat.h>
|
|
#include <fcntl.h>
|
|
#include <string.h>
|
|
#include <time.h>
|
|
#include "delay.h"
|
|
|
|
#define N_INIT 10000000
|
|
double nspw; /* nsec per work */
|
|
|
|
void ndelay_init(int verbose)
|
|
{
|
|
struct timeval start, end;
|
|
|
|
//clock_gettime(TIMER_KIND, &start);
|
|
gettimeofday(&start, NULL);
|
|
|
|
#pragma omp parallel
|
|
{
|
|
asmloop(N_INIT);
|
|
}
|
|
|
|
//clock_gettime(TIMER_KIND, &end);
|
|
gettimeofday(&end, NULL);
|
|
|
|
nspw = DIFFUSEC(end, start) * 1000 / (double)N_INIT;
|
|
if (verbose) {
|
|
pr_debug("nspw=%f\n", nspw);
|
|
}
|
|
}
|
|
|
|
void ndelay(long delay_nsec)
|
|
{
|
|
if (delay_nsec < 0) {
|
|
printf("delay_nsec < 0\n");
|
|
return;
|
|
}
|
|
#pragma omp parallel
|
|
{
|
|
asmloop(delay_nsec / nspw);
|
|
}
|
|
}
|
|
|
|
static double cycpw; /* cyc per work */
|
|
|
|
void cdlay_init(void)
|
|
{
|
|
unsigned long start, end;
|
|
|
|
start = rdtsc_light();
|
|
#define N_INIT 10000000
|
|
asmloop(N_INIT);
|
|
end = rdtsc_light();
|
|
cycpw = (end - start) / (double)N_INIT;
|
|
}
|
|
|
|
void cdelay(long delay_cyc)
|
|
{
|
|
if (delay_cyc < 0) {
|
|
return;
|
|
}
|
|
asmloop(delay_cyc / cycpw);
|
|
}
|