WhyCan Forum(哇酷开发者社区)

[    4.016823] rtc-pcf8563 0-0051: low voltage detected, date/time is not reliable.
[    4.038809] dwmac-sun8i 1c30000.ethernet eth0: device MAC address ce:61:db:3b:bc:44
[    4.050021] Generic PHY stmmac-0:01: attached PHY driver [Generic PHY] (mii_bus:phy_addr=stmmac-0:01, irq=-1)
[    4.063362] dwmac-sun8i 1c30000.ethernet eth0: No MAC Management Counters available
[    4.071209] dwmac-sun8i 1c30000.ethernet eth0: PTP not supported by HW
[    5.314400] jffs2: notice: (94) jffs2_get_inode_nodes: Wrong magic bitmask 0x0000 in node header at 0x10000c.
[    7.212177] dwmac-sun8i 1c30000.ethernet eth0: Link is Up - 100Mbps/Full - flow control off
[    9.508975] usb 2-1: new low-speed USB device number 2 using ohci-platform
[    9.948970] usb 2-1: device not accepting address 2, error -62
[   10.148999] usb 2-1: new low-speed USB device number 3 using ohci-platform
[   10.588951] usb 2-1: device not accepting address 3, error -62
[   10.594977] usb usb2-port1: unable to enumerate USB device

#
# /etc/init.d/S41dhcpcd restart
Stopping dhcpcd...
stopped /sbin/dhcpcd (pid 226)
Starting dhcpcd...
no interfaces have a carrier
forked to background, child pid 255
# 
# 
# 
# /etc/init.d/S01syslogd restart
Stopping syslogd: OK
Starting syslogd: OK
# 
# 
# 
#  /etc/init.d/S50dropbear restart
Stopping dropbear sshd: OK
Starting dropbear sshd: OK
# 
# 
# 
# ps
PID   USER     COMMAND
    1 root     init
    2 root     [kthreadd]
    3 root     [rcu_gp]
    4 root     [rcu_par_gp]
    5 root     [kworker/0:0-pm]
    6 root     [kworker/0:0H-kb]
    7 root     [kworker/u8:0-br]
    8 root     [mm_percpu_wq]
    9 root     [ksoftirqd/0]
   10 root     [rcu_sched]
   11 root     [migration/0]
   12 root     [cpuhp/0]
   13 root     [cpuhp/1]
   14 root     [migration/1]
   15 root     [ksoftirqd/1]
   16 root     [kworker/1:0-pm]
   17 root     [kworker/1:0H-kb]
   18 root     [cpuhp/2]
   19 root     [migration/2]
   20 root     [ksoftirqd/2]
   21 root     [kworker/2:0-eve]
   22 root     [kworker/2:0H-kb]
   23 root     [cpuhp/3]
   24 root     [migration/3]
   25 root     [ksoftirqd/3]
   26 root     [kworker/3:0-pm]
   27 root     [kworker/3:0H-kb]
   28 root     [kdevtmpfs]
   29 root     [netns]
   30 root     [kworker/0:1-eve]
   31 root     [kworker/1:1-rcu]
   32 root     [kworker/2:1-mm_]
   33 root     [oom_reaper]
   34 root     [writeback]
   35 root     [kcompactd0]
   36 root     [crypto]
   37 root     [kblockd]
   38 root     [ata_sff]
   39 root     [watchdogd]
   40 root     [rpciod]
   41 root     [kworker/u9:0]
   42 root     [xprtiod]
   43 root     [kswapd0]
   44 root     [nfsiod]
   46 root     [kworker/u8:1-ev]
   68 root     [spi0]
   69 root     [kworker/3:1-mm_]
   70 root     [irq/23-sunxi-mm]
   71 root     [irq/24-sunxi-mm]
   72 root     [kworker/1:2-eve]
   73 root     [irq/25-sunxi-mm]
   74 root     [kworker/1:3-mm_]
   75 root     [kworker/1:4]
   76 root     [kworker/1:1H-kb]
   77 root     [kworker/0:1H-kb]
   79 root     [kworker/3:2-mm_]
   80 root     [kworker/3:1H-kb]
   81 root     [kworker/3:2H]
   82 root     [jbd2/mmcblk0p2-]
   83 root     [ext4-rsv-conver]
   84 root     [kworker/0:2H]
   86 root     [kworker/2:1H-kb]
  104 root     /sbin/klogd -n
  131 root     [kworker/u8:2-ev]
  134 root     [kworker/u8:3]
  144 root     [cfg80211]
  152 root     -/bin/sh
  155 root     [kworker/2:2H]
  156 root     [kworker/0:2-eve]
  157 root     [kworker/2:2]
  159 root     [brcmf_wq/mmc1:0]
  161 root     [brcmf_wdog/mmc1]
  162 root     [ksdioirqd/mmc1]
  183 root     wpa_supplicant -i wlan0 -D wext -c /etc/wpa_supplicant.conf -B
  255 root     /sbin/dhcpcd -f /etc/dhcpcd.conf
  263 root     /sbin/syslogd -n
  274 root     /usr/sbin/dropbear -R
  276 root     ps
# 

$ ARCH=arm CROSS_COMPILE=arm-linux-gnueabihf- make -C ~/A33/mainline/linux  M=${PWD}  modules
make: Entering directory '/home/ubuntu/A33/mainline/linux'
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_debug.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/sdio_sif_esp.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/spi_sif_esp.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_io.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_file.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_main.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_sip.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_ext.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_ctrl.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_mac80211.o
/home/ubuntu/A33/mainline/esp8089/esp_mac80211.c: In function ‘beacon_tim_init’:
/home/ubuntu/A33/mainline/esp8089/esp_mac80211.c:372:2: warning: ‘memset’ used with constant zero length parameter; this could be due to transposed parameters [-Wmemset-transposed-args]
  memset(beacon_tim_saved, BEACON_TIM_SAVE_MAX, 0);
  ^~~~~~
/home/ubuntu/A33/mainline/esp8089/esp_mac80211.c: In function ‘hw_scan_done’:
/home/ubuntu/A33/mainline/esp8089/esp_mac80211.c:924:9: warning: ISO C90 forbids mixed declarations and code [-Wdeclaration-after-statement]
         struct cfg80211_scan_info info = {
         ^~~~~~
/home/ubuntu/A33/mainline/esp8089/esp_mac80211.c: In function ‘hw_scan_timeout_report’:
/home/ubuntu/A33/mainline/esp8089/esp_mac80211.c:958:9: warning: ISO C90 forbids mixed declarations and code [-Wdeclaration-after-statement]
         struct cfg80211_scan_info info = {
         ^~~~~~
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_utils.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/esp_pm.o
  CC [M]  /home/ubuntu/A33/mainline/esp8089/testmode.o
  LD [M]  /home/ubuntu/A33/mainline/esp8089/esp8089.o
  Building modules, stage 2.
  MODPOST 1 modules
WARNING: "ieee80211_rx_napi" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_queue_work" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_hdrlen" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_beacon_get_tim" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_unregister_hw" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_scan_completed" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "wiphy_rfkill_start_polling" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_stop_queues" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_ready_on_channel" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_tx_status" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_alloc_hw_nm" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_wake_queues" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_remain_on_channel_expired" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_stop_tx_ba_cb_irqsafe" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "wiphy_rfkill_set_hw_state" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_get_buffered_bc" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_register_hw" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_start_tx_ba_session" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_free_hw" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_start_tx_ba_cb_irqsafe" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
WARNING: "ieee80211_stop_tx_ba_session" [/home/ubuntu/A33/mainline/esp8089/esp8089.ko] undefined!
  CC      /home/ubuntu/A33/mainline/esp8089/esp8089.mod.o
  LD [M]  /home/ubuntu/A33/mainline/esp8089/esp8089.ko
make: Leaving directory '/home/ubuntu/A33/mainline/linux'

wget https://developer.download.nvidia.com/compute/cuda/repos/ubuntu1804/x86_64/cuda-ubuntu1804.pin
sudo mv cuda-ubuntu1804.pin /etc/apt/preferences.d/cuda-repository-pin-600
wget http://developer.download.nvidia.com/compute/cuda/10.1/Prod/local_installers/cuda-repo-ubuntu1804-10-1-local-10.1.243-418.87.00_1.0-1_amd64.deb
sudo dpkg -i cuda-repo-ubuntu1804-10-1-local-10.1.243-418.87.00_1.0-1_amd64.deb
sudo apt-key add /var/cuda-repo-10-1-local-10.1.243-418.87.00/7fa2af80.pub
sudo apt-get update
sudo apt-get -y install cuda

#include "cuda_runtime.h"
#include <stdio.h>
#include <stdlib.h>
#include <iostream>
#include <cstdio>
#include <chrono>

typedef std::chrono::high_resolution_clock Clock;

#define ITER 65535

// CPU version of the vector add function
void vector_add_cpu(int *a, int *b, int *c, int n) {
    int i;

    // Add the vector elements a and b to the vector c
    for (i = 0; i < n; ++i) {
    c[i] = a[i] + b[i];
    }
}

// GPU version of the vector add function
__global__ void vector_add_gpu(int *gpu_a, int *gpu_b, int *gpu_c, int n) {
    int i = threadIdx.x;
    // No for loop needed because the CUDA runtime
    // will thread this ITER times
    gpu_c[i] = gpu_a[i] + gpu_b[i];
}

int main() {

    int *a, *b, *c;
    int *gpu_a, *gpu_b, *gpu_c;

    a = (int *)malloc(ITER * sizeof(int));
    b = (int *)malloc(ITER * sizeof(int));
    c = (int *)malloc(ITER * sizeof(int));

    // We need variables accessible to the GPU,
    // so cudaMallocManaged provides these
    cudaMallocManaged(&gpu_a, ITER * sizeof(int));
    cudaMallocManaged(&gpu_b, ITER * sizeof(int));
    cudaMallocManaged(&gpu_c, ITER * sizeof(int));

    for (int i = 0; i < ITER; ++i) {
        a[i] = i;
        b[i] = i;
        c[i] = i;
    }

    // Call the CPU function and time it
    auto cpu_start = Clock::now();
    vector_add_cpu(a, b, c, ITER);
    auto cpu_end = Clock::now();
    std::cout << "vector_add_cpu: "
    << std::chrono::duration_cast<std::chrono::nanoseconds>(cpu_end - cpu_start).count()
    << " nanoseconds.\n";

    // Call the GPU function and time it
    // The triple angle brakets is a CUDA runtime extension that allows
    // parameters of a CUDA kernel call to be passed.
    // In this example, we are passing one thread block with ITER threads.
    auto gpu_start = Clock::now();
    vector_add_gpu <<<1, ITER>>> (gpu_a, gpu_b, gpu_c, ITER);
    cudaDeviceSynchronize();
    auto gpu_end = Clock::now();
    std::cout << "vector_add_gpu: "
    << std::chrono::duration_cast<std::chrono::nanoseconds>(gpu_end - gpu_start).count()
    << " nanoseconds.\n";

    // Free the GPU-function based memory allocations
    cudaFree(a);
    cudaFree(b);
    cudaFree(c);

    // Free the CPU-function based memory allocations
    free(a);
    free(b);
    free(c);

    return 0;
}

INC=-I/usr/local/cuda/include
NVCC=/usr/local/cuda/bin/nvcc
NVCC_OPT=-std=c++11

all:
    $(NVCC) $(NVCC_OPT) gpu-example.cu-o gpu-example

clean:
    -rm -f gpu-example

gpu-test$ ./gpu-example 
vector_add_cpu: 1370132 nanoseconds.
vector_add_gpu: 6445 nanoseconds.