Skip to content
New issue

Have a question about this project? Sign up for a free GitHub account to open an issue and contact its maintainers and the community.

By clicking “Sign up for GitHub”, you agree to our terms of service and privacy statement. We’ll occasionally send you account related emails.

Already on GitHub? Sign in to your account

Fix synchronization issues in RNG checkpointing utils #5273

Merged
merged 4 commits into from
Jan 16, 2024

Conversation

szkarpinski
Copy link
Collaborator

@szkarpinski szkarpinski commented Jan 9, 2024

Category:

Bug fix (non-breaking change which fixes an issue)

Description:

This PR fixes two synchronization bugs pointed out by @mzient . Both problems happen when you're restoring from checkpoint in random GPU operators and are due to lack of synchronization after H2D & D2D copies.

PS. Another problem pointed out was that synchronization between SaveState and Serialize is handled by the pipeline and not by those functions. This is a design problem and I added a TODO to fix it. I'm currently reworking how synchronization works when a checkpoint is saved, so I'll fix it there.

Additional information:

Affected modules and functionalities:

RngCheckpointingUtils

Key points relevant for the review:

Tests:

  • Existing tests apply
  • New tests added
    • Python tests
    • GTests
    • Benchmark
    • Other
  • N/A

Checklist

Documentation

  • Existing documentation applies
  • Documentation updated
    • Docstring
    • Doxygen
    • RST
    • Jupyter
    • Other
  • N/A

DALI team only

Requirements

  • Implements new requirements
  • Affects existing requirements
  • N/A

REQ IDs: N/A

JIRA TASK: DALI-3777

Signed-off-by: Szymon Karpiński <skarpinski@nvidia.com>
Signed-off-by: Szymon Karpiński <skarpinski@nvidia.com>
Signed-off-by: Szymon Karpiński <skarpinski@nvidia.com>
Signed-off-by: Szymon Karpiński <skarpinski@nvidia.com>
@szkarpinski szkarpinski marked this pull request as ready for review January 11, 2024 11:54
@mzient mzient self-assigned this Jan 12, 2024
Comment on lines +62 to +64
CUDA_CALL(cudaMemcpyAsync(states_, other.states_, sizeof(curandState) * len_,
cudaMemcpyDeviceToDevice, cudaStreamDefault));
CUDA_CALL(cudaStreamSynchronize(cudaStreamDefault));
Copy link
Contributor

Choose a reason for hiding this comment

The reason will be displayed to describe this comment to others. Learn more.

It will do for a quick bug fix, but it would probably be better to use a proper stream.

@szkarpinski
Copy link
Collaborator Author

!build

@dali-automaton
Copy link
Collaborator

CI MESSAGE: [12105479]: BUILD STARTED

@dali-automaton
Copy link
Collaborator

CI MESSAGE: [12105479]: BUILD FAILED

@dali-automaton
Copy link
Collaborator

CI MESSAGE: [12105479]: BUILD PASSED

@szkarpinski szkarpinski merged commit b98cba1 into NVIDIA:main Jan 16, 2024
7 checks passed
stiepan pushed a commit that referenced this pull request Jan 16, 2024
This PR fixes two synchronization bugs. Both problems happen when you're restoring from checkpoint in random GPU operators and are due to lack of synchronization after H2D & D2D copies.

---------

Signed-off-by: Szymon Karpiński <skarpinski@nvidia.com>
Sign up for free to join this conversation on GitHub. Already have an account? Sign in to comment
Labels
None yet
Projects
None yet
Development

Successfully merging this pull request may close these issues.

4 participants