“Christopher
|
665d0a4f89
|
Added example of removing cooperative groups
|
2024-05-02 02:09:57 +00:00 |
|
Jane Illarionova
|
d6d0d50627
|
fix typo
|
2024-05-02 00:18:55 +00:00 |
|
Jane Illarionova
|
d0e5fea2dd
|
update residual_forward to use util functions
|
2024-05-02 00:17:47 +00:00 |
|
Jane Illarionova
|
7203c7875f
|
remove int cast
|
2024-05-02 00:17:47 +00:00 |
|
Jane Illarionova
|
4698164e3e
|
update train to multiply block size
|
2024-05-02 00:17:47 +00:00 |
|
Jane Illarionova
|
52b4dd02a1
|
update residual forward to allow kernels to use both types
|
2024-05-02 00:17:47 +00:00 |
|
Jane Illarionova
|
32df703a05
|
Update train_gpt2.cu
|
2024-05-02 00:17:47 +00:00 |
|
Jane Illarionova
|
4ffcf5b90a
|
Update residual_forward.cu
|
2024-05-02 00:17:47 +00:00 |
|
Jane Illarionova
|
3de3c53ba9
|
update kernel with util functions
|
2024-05-01 23:58:49 +00:00 |
|
Jane Illarionova
|
d98e5ae859
|
remove int casting
|
2024-05-01 23:36:59 +00:00 |
|
Jane Illarionova
|
e9a80b5d84
|
update ceildiv for gelu_backward
|
2024-05-01 23:36:59 +00:00 |
|
Jane Illarionova
|
7746217433
|
update gelu backward rto allow all kernels to use both types
|
2024-05-01 23:36:59 +00:00 |
|
Jane Illarionova
|
ab2de05a13
|
Update train_gpt2.cu
|
2024-05-01 23:36:59 +00:00 |
|
Jane Illarionova
|
80072802d7
|
Create gelu_backward.cu
|
2024-05-01 23:36:59 +00:00 |
|
Andrej
|
4dd1ab43de
|
Merge pull request #328 from karpathy/feature/fp32_weight_master_copy
feature/fp32 weight master copy
|
2024-05-01 16:07:19 -07:00 |
|
Andrej Karpathy
|
c177c2694c
|
make nice and print
|
2024-05-01 23:06:23 +00:00 |
|
Andrej Karpathy
|
795f8b690c
|
fixes to keep master copy in fp32 of weights optionally
|
2024-05-01 22:50:22 +00:00 |
|
Yusheng (Ethan) Su
|
24abcbf6d2
|
Merge branch 'karpathy:master' into master
|
2024-05-02 02:19:16 +04:00 |
|
Yusheng Su
|
ac2d635007
|
add required package (requests) into requirements.txt
|
2024-05-02 02:11:38 +04:00 |
|
Andrej Karpathy
|
fd474feec8
|
Merge branch 'fp32-weights' of https://github.com/ngc92/llm.c
|
2024-05-01 22:02:55 +00:00 |
|
Erik Schultheis
|
df9f0efde6
|
updated letter and properly free buffer
|
2024-05-02 01:00:36 +03:00 |
|
Andrej
|
f4f7a987e7
|
Merge pull request #324 from eymay/init_weights_from_scratch
Refactoring parameter size filling
|
2024-05-01 14:50:39 -07:00 |
|
Erik Schultheis
|
e9c76a1753
|
option to keep weights as fp32
|
2024-05-02 00:11:07 +03:00 |
|
Andrej
|
ab95a11190
|
Merge pull request #325 from ngc92/dev-cuda-utils
mixed precision utilities for dev/cuda
|
2024-05-01 12:54:54 -07:00 |
|
Erik Schultheis
|
b42db706b2
|
this kernel will be released later, sorry for the spoiler :)
|
2024-05-01 22:47:24 +03:00 |
|
Erik Schultheis
|
91bc72d0c0
|
fixup
|
2024-05-01 22:40:26 +03:00 |
|
Erik Schultheis
|
06980b6b2f
|
mixed precision utilities for dev/cuda
|
2024-05-01 22:35:55 +03:00 |
|
Andrej
|
d37639a8cb
|
Merge pull request #316 from rosslwheeler/designated_init_fix
uint and designated initializers non-standard for C++ / Cuda
|
2024-05-01 12:13:12 -07:00 |
|
Andrej
|
be5cee21e6
|
Merge pull request #317 from ChrisDryden/patch-5
Removed detail about layernorm inputs being f32, no longer the case
|
2024-05-01 12:00:01 -07:00 |
|
Andrej
|
38b478d8f9
|
Merge pull request #323 from karpathy/feature/cudnn
feature/cudnn for flash-attention
|
2024-05-01 11:34:16 -07:00 |
|
Andrej Karpathy
|
7d0042d574
|
make training data configurable and also dont move the engire dataset to device that is not a good idea
|
2024-05-01 18:15:10 +00:00 |
|
Andrej Karpathy
|
8aa9a9ed53
|
and also profile lol
|
2024-05-01 17:56:01 +00:00 |
|
Andrej Karpathy
|
1ed9381fd0
|
fix cudnnDestroy outside of ifdef
|
2024-05-01 17:55:36 +00:00 |
|
Andrej Karpathy
|
69d40ebfff
|
add readme and search for cudd in home dir
|
2024-05-01 17:43:50 +00:00 |
|
Andrej Karpathy
|
35640651b3
|
updates to makefile: docs, override, etc
|
2024-05-01 17:32:52 +00:00 |
|
Andrej Karpathy
|
04718fbbd1
|
round 1 of small fixes for cudnn support
|
2024-05-01 17:07:10 +00:00 |
|
ademeure
|
1147983b8c
|
Add missing cudnnDestroy() calls
|
2024-05-01 17:19:51 +01:00 |
|
ademeure
|
d9e7a0a378
|
Fixed profile_gpt2.cu/test_gpt2.cu for cuDNN
|
2024-05-01 17:03:28 +01:00 |
|
ademeure
|
2b540b61da
|
attention_forward.cu ~matches train_gpt2cu & allocate less memory for stats in "att"
|
2024-05-01 16:53:01 +01:00 |
|
ademeure
|
be54842622
|
Rename lowp_float to floatX in /dev/cuda/attention_forward.cu
|
2024-05-01 15:43:28 +01:00 |
|
ademeure
|
c778dc0098
|
slightly increase wte threshold to make test_gpt2.cu pass (?)
|
2024-05-01 15:40:30 +01:00 |
|
ademeure
|
57c09529d9
|
Merge branch 'cudnn_try2' of https://github.com/ademeure/llm.c into cudnn_try2
|
2024-05-01 15:32:13 +01:00 |
|
ademeure
|
7beff72f5f
|
Add makefile changes for cuDNN
|
2024-05-01 15:31:30 +01:00 |
|
ademeure
|
c4ecc04dc3
|
Merge remote-tracking branch 'karpathy/master' into cudnn_try2
|
2024-05-01 15:30:00 +01:00 |
|
ademeure
|
d508463ad7
|
Merge remote-tracking branch 'origin/cudnn_try2' into cudnn_try2
|
2024-05-01 15:27:07 +01:00 |
|
ademeure
|
d42ee0d925
|
Cleanup + do not allocate gradient preatt memory with cuDNN + allocate as small a cuDNN workspace as possible
|
2024-05-01 15:26:25 +01:00 |
|
ademeure
|
61ad4b15ab
|
Fully working forward+backward cuDNN BF16 Flash Attention in train_gpt2.cu!
|
2024-05-01 15:02:47 +01:00 |
|
Chris Dryden
|
1806062a62
|
Removed detail about layernorm inputs being f32, no longer the case
|
2024-04-30 22:01:14 -07:00 |
|
Ross Wheeler
|
229d70b2d5
|
uint and designated initializers non-standard for C++
uint isn't defined by the MS compiler and designated initializers aren't part of C++ until C++ 20.
|
2024-04-30 18:46:54 -07:00 |
|
Andrej
|
40da8cf233
|
Merge pull request #314 from jrhemstad/patch-3
Add llm.cpp fork to README
|
2024-04-30 17:03:25 -07:00 |
|