#include <unistd.h>
#include <stdint.h>
#include <stdio.h>
#include <stdlib.h>
#include <string.h>
#include <errno.h>
#include <fcntl.h>
#include <g2d.h>
#include <linux/fb.h>
#include <linux/ipu.h>
#include <ncurses.h>
#include <omp.h>
#include <pthread.h>
#include <semaphore.h>
#include <sys/ioctl.h>
#include <sys/ipc.h>
#include <sys/mman.h>
#include <sys/msg.h>
#include <sys/prctl.h>
#include <sys/time.h>
int omp(const uint8_t * a, uint8_t * restrict n, uint32_t sx, uint32_t sy) {
uint32_t x,y;
int rv = 0;
#pragma omp parallel for num_threads(4)
for (y = 1; y<(sy-1); y++) {
for (x = 1; x<(sx-1); x++) {
n[y*sx+x] += (a[y*sx+x-1] + a[y*sx+x+1] + a[y*sx+x-sx] + a[y*sx+x+sx]);
}
rv += n[y*sx];
}
return 0;
}
int main(int argc, char **argv) {
uint8_t *output_image;
void * g2d_handle;
struct g2d_buf *s_buf;
int fbfd = 0;
uint8_t *fbp = 0;
struct fb_var_screeninfo vinfo;
struct fb_fix_screeninfo finfo;
long int screensize;
int rv;
//
output_image = malloc( 1456 * 1088* 4 );
initscr();
cbreak();
noecho();
g2d_open(&g2d_handle);
s_buf = g2d_alloc(1456 * 1088 * 4, 0);
fbfd = open("/dev/fb0", O_RDWR);
if (fbfd == -1) {
perror("Error: cannot open framebuffer device");
exit(1);
}
if (ioctl(fbfd, FBIOGET_FSCREENINFO, &finfo) == -1) {
perror("Error reading fixed information");
exit(2);
}
if (ioctl(fbfd, FBIOGET_VSCREENINFO, &vinfo) == -1) {
perror("Error reading variable information");
exit(3);
}
screensize = vinfo.xres * vinfo.yres * vinfo.bits_per_pixel / 8;
fbp = (char *)mmap(0, screensize, PROT_READ | PROT_WRITE, MAP_SHARED, fbfd, 0);
rv = omp((uint8_t*)output_image, (uint8_t*)s_buf->buf_vaddr, 1456, 1088);
free(output_image);
munmap(fbp,screensize);
g2d_free(s_buf);
g2d_close(g2d_handle);
return rv;
}
12.03.2019 14:20 
19.03.2019 00:45
