44d63cd4b0
update common submodule
2019-08-15 13:57:17 +02:00
30dff972f2
several fixes for villas-fpga-pipe
2019-08-15 13:55:39 +02:00
f6a78bea69
dma: add dump() method
2019-08-15 13:54:58 +02:00
Hatim Kanchwala
bf74db8e79
Debug update
2019-06-24 12:11:44 -04:00
3326c83fc7
add note to cite our publication
2018-09-20 11:19:23 +02:00
5361c1d20d
move gpu module to top level directory
2018-08-21 15:53:47 +02:00
3f119896e9
ci: some tweaks to fix unit-tests
2018-08-21 15:29:37 +02:00
d191a86c18
do not call copy-ctor of villas::HostRamAllocator
2018-08-21 14:25:42 +02:00
8b45a8bcac
fix include paths
2018-08-21 14:25:20 +02:00
ea4b453250
tests: remove obsolete unit tests which have been moved to VILLAScommon
2018-08-21 13:54:21 +02:00
2112038d70
Merge branch 'feature/hls-rtds2gpu' into develop
2018-08-21 13:51:32 +02:00
5c7f167617
pipe: rename streamer to pipe ( closes #19 )
2018-08-21 13:40:38 +02:00
106d215dd2
fix gdrcopy submodule
2018-08-21 13:31:56 +02:00
4158ddb792
gpu: fix include paths and some linker settings
2018-08-21 13:28:07 +02:00
76b1695586
move more code to VILLAScommon repo
2018-08-21 13:27:04 +02:00
Daniel Krebs
96cd71a87e
gpu/gdrcopy: rebase on current upstream master and update
2018-08-21 13:12:51 +02:00
5e8c602c8d
ci: use Centos 7 based Docker Image with CUDA dev env from Nvidia
2018-08-21 12:39:39 +02:00
d0ff063e70
ci: use relative path in gitmodules for proper access rights
2018-08-21 12:24:50 +02:00
9b0c0226c3
update common submodule
2018-08-21 12:22:51 +02:00
f8de9425fe
streamer: use new memory api
2018-08-21 11:10:09 +02:00
df89b63368
fix include paths
2018-08-21 11:07:53 +02:00
de566d441d
move common code to VILLAScommon submodule
2018-08-21 01:14:18 +02:00
Daniel Krebs
b2698c8bd5
rtds2gpu: update register type to work for more complex payloads
2018-07-26 16:49:06 +02:00
Daniel Krebs
c44aedd6a9
gpu: update to recent GDRcopy
2018-07-20 16:52:09 +02:00
Daniel Krebs
26abf44d2f
villas/memory: add sanity check to deny allocating zero-sized memory
2018-07-20 16:50:54 +02:00
Daniel Krebs
8a06e96e92
gpu: always allocate page-sized chunks, then use LinearAllocator
...
This was neccessary in order to make the memory available via GDRcopy
when multiple small allocations were made. cudaMalloc() would return
multiple memory chunks located in the same GPU page, which GDRcopy
pretty much dislikes (`gdrdrv:offset != 0 is not supported`).
As a side effect, this will keep the number of BAR-mappings done
via GDRcopy low, because they seem to be quite limited.
2018-07-20 16:46:55 +02:00
Daniel Krebs
375b6b5cd3
common/memory: let allocators own a memory block
...
This is useful when we sub-delegate management of a memory block
to another allocator.
2018-07-20 16:44:50 +02:00
Daniel Krebs
0cdc05c3d5
rtds2gpu: add struct for memory layout of rtds2gpu buffer
2018-07-11 16:06:48 +02:00
Daniel Krebs
98c98b6855
tests: add missing gpu kernels
2018-07-11 14:00:20 +02:00
63a1eb2f7f
remove some obsolete C code files
2018-06-25 17:22:31 +02:00
7409d2024d
add more copyright / license headers
2018-06-25 17:03:09 +02:00
acd9412f6e
add Daniel to README
2018-06-25 16:43:15 +02:00
9d57983934
added submodule to VILLASfpga-hardware repo
2018-06-25 16:38:48 +02:00
55c9131958
update Fedora version in Dockerfile
2018-06-25 16:01:54 +02:00
fb6a7178b7
add pcimem.c
2018-06-25 16:01:38 +02:00
7fd6599ea6
update copyright years
2018-06-25 15:33:14 +02:00
63e523de46
do not store bitstreams here
2018-06-25 15:27:06 +02:00
Daniel Krebs
d853d5e0d3
wip GPU RTT
2018-06-06 09:55:14 +02:00
Daniel Krebs
f7781d47af
tests/rtds2gpu: cleanup
2018-06-05 14:56:43 +02:00
Daniel Krebs
2a56f5ff13
tests/rtds2gpu: fix doorbell offset
2018-06-05 14:48:35 +02:00
Daniel Krebs
49f0c2e0c4
unit test RTT via CPU to/from RTDS works!
2018-06-04 19:06:36 +02:00
Daniel Krebs
92bfe849b4
ips/rtds2gpu: use new connect interface
2018-06-04 17:36:36 +02:00
Daniel Krebs
194c4e3eef
etc: update fpga.json with changes related to stream routing
2018-06-04 17:36:36 +02:00
Daniel Krebs
f413712b86
gpu2rtds: unit test working
2018-06-04 17:36:36 +02:00
Daniel Krebs
93fe1390d6
fix wrong usage of reinterpret_cast in ips and tests
2018-06-04 17:36:36 +02:00
Daniel Krebs
010e0c3681
hls: add base HLS IP and enable virtual multi-inheritance
...
Virtual inheritance is required because (for example) the Rtds2Gpu
IP inherits from Hls and IpNode who both inherit from IpCore.
2018-06-04 17:36:36 +02:00
Daniel Krebs
5c67dc3727
rtds2gpu: update vlnv to match v1.1 and adapt config to new bitstream
2018-06-04 17:36:15 +02:00
Daniel Krebs
28458fdf8a
update rtds2gpu HLS IP to v1.1
...
- better tested IP (testbenches)
- detect invalid frame sizes
- more status reporting
2018-06-04 17:36:15 +02:00
Daniel Krebs
bf286568dd
rtds2gpu IP works
2018-06-04 17:36:15 +02:00
Daniel Krebs
b03b94d754
ip-node: fix wrong cast and add more sanity checks
2018-06-04 17:31:25 +02:00
